Home
last modified time | relevance | path

Searched refs:vstate (Results 1 – 10 of 10) sorted by relevance

/linux/kernel/bpf/
H A Dlog.c700 void print_verifier_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate, in print_verifier_state() argument
703 const struct bpf_func_state *state = vstate->frame[frameno]; in print_verifier_state()
782 if (vstate->acquired_refs && vstate->refs[0].id) { in print_verifier_state()
783 verbose(env, " refs=%d", vstate->refs[0].id); in print_verifier_state()
784 for (i = 1; i < vstate->acquired_refs; i++) in print_verifier_state()
785 if (vstate->refs[i].id) in print_verifier_state()
786 verbose(env, ",%d", vstate->refs[i].id); in print_verifier_state()
803 void print_insn_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate, in print_insn_state() argument
813 print_verifier_state(env, vstate, frameno, false); in print_insn_state()
H A Dverifier.c3224 struct bpf_verifier_state *vstate = env->cur_state; in check_reg_arg() local
3225 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_reg_arg()
3801 struct bpf_verifier_state *vstate = env->cur_state; in mark_reg_stack_read() local
3802 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_reg_stack_read()
3871 struct bpf_verifier_state *vstate = env->cur_state; in check_stack_read_fixed_off() local
3872 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_stack_read_fixed_off()
4219 struct bpf_verifier_state *vstate in check_stack_arg_read() local
6648 struct bpf_verifier_state *vstate = env->cur_state; check_load_mem() local
6694 struct bpf_verifier_state *vstate = env->cur_state; check_store_reg() local
9401 mark_pkt_end(struct bpf_verifier_state * vstate,int regn,bool range_open) mark_pkt_end() argument
9477 struct bpf_verifier_state *vstate = env->cur_state; release_reference() local
14373 struct bpf_verifier_state *vstate = env->cur_state; sanitize_ptr_alu() local
14462 struct bpf_verifier_state *vstate = env->cur_state; sanitize_mark_insn_seen() local
14581 struct bpf_verifier_state *vstate = env->cur_state; adjust_ptr_min_max_vals() local
15739 struct bpf_verifier_state *vstate = env->cur_state; adjust_reg_min_max_vals() local
16114 find_good_pkt_pointers(struct bpf_verifier_state * vstate,struct bpf_reg_state * dst_reg,enum bpf_reg_type type,bool range_right_open) find_good_pkt_pointers() argument
16721 mark_ptr_or_null_regs(struct bpf_verifier_state * vstate,u32 regno,bool is_null) mark_ptr_or_null_regs() argument
16868 collect_linked_regs(struct bpf_verifier_env * env,struct bpf_verifier_state * vstate,u32 id,struct linked_regs * linked_regs) collect_linked_regs() argument
16900 sync_linked_regs(struct bpf_verifier_env * env,struct bpf_verifier_state * vstate,struct bpf_reg_state * known_reg,struct linked_regs * linked_regs) sync_linked_regs() argument
18310 struct bpf_verifier_state *vstate = env->cur_state; do_check_insn() local
[all...]
H A Ddiagnostics.c1551 struct bpf_verifier_state *vstate = env->cur_state; in target_to_reg() local
1554 state = target->frameno <= vstate->curframe ? vstate->frame[target->frameno] : NULL; in target_to_reg()
1582 struct bpf_verifier_state *vstate = env->cur_state; in reg_to_target() local
1586 for (frame = 0; frame <= vstate->curframe; frame++) { in reg_to_target()
1587 struct bpf_func_state *state = vstate->frame[frame]; in reg_to_target()
/linux/arch/riscv/kernel/
H A Dsignal.c93 riscv_v_vstate_save(&current->thread.vstate, regs); in save_v_state()
97 err = __copy_to_user(&state->v_state, &current->thread.vstate, in save_v_state()
102 err |= __copy_to_user(datap, current->thread.vstate.datap, riscv_v_vsize); in save_v_state()
129 err = __copy_from_user(&current->thread.vstate, &state->v_state, in __restore_v_state()
142 return copy_from_user(current->thread.vstate.datap, datap, riscv_v_vsize); in __restore_v_state()
H A Dprocess.c199 kfree(current->thread.vstate.datap); in flush_thread()
200 memset(&current->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in flush_thread()
221 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
/linux/tools/perf/util/
H A Dpmus.c593 static int perf_pmus__print_pmu_events__callback(void *vstate, in perf_pmus__print_pmu_events__callback()
596 struct events_callback_state *state = vstate; in perf_pmus__print_pmu_events__callback()
575 perf_pmus__print_pmu_events__callback(void * vstate,struct pmu_event_info * info) perf_pmus__print_pmu_events__callback() argument
/linux/include/linux/
H A Dbpf_verifier.h1496 void print_verifier_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate,
1498 void print_insn_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate,
/linux/drivers/gpu/drm/amd/pm/
H A Damdgpu_dpm.c1002 struct amd_vce_state *vstate = NULL; in amdgpu_dpm_get_vce_clock_state() local
1008 vstate = pp_funcs->get_vce_clock_state(adev->powerplay.pp_handle, in amdgpu_dpm_get_vce_clock_state()
1012 return vstate; in amdgpu_dpm_get_vce_clock_state()
/linux/net/netfilter/
H A Dnf_tables_api.c141 if (chain->vstate.depth >= ctx->level && in nft_chain_vstate_valid()
142 chain->vstate.hook_mask[type] & BIT(hooknum)) in nft_chain_vstate_valid()
4160 memset(&chain->vstate, 0, sizeof(chain->vstate)); in nft_chain_vstate_update()
4170 chain->vstate.hook_mask[type] |= BIT(hooknum); in nft_chain_vstate_update()
4171 if (chain->vstate.depth < ctx->level) in nft_chain_vstate_update()
4172 chain->vstate.depth = ctx->level; in nft_chain_vstate_update()
4251 memset(&chain->vstate, 0, sizeof(chain->vstate)); in nft_table_validate()
/linux/include/net/netfilter/
H A Dnf_tables.h1153 struct nft_chain_validate_state vstate; member