| /linux/arch/riscv/include/asm/ |
| H A D | vector.h | 306 static inline void riscv_v_vstate_save(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_save() argument
310 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save()
315 static inline void riscv_v_vstate_restore(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_restore() argument
319 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore()
387 riscv_v_vstate_save(&prev->thread.vstate, regs); in __switch_to_vector()
419 #define riscv_v_vstate_save(vstate, regs) do {} while (0) argument
420 #define riscv_v_vstate_restore(vstate, regs) do {} while (0) argument
|
| H A D | processor.h | 117 struct __riscv_v_ext_state vstate; member
|
| /linux/arch/riscv/kernel/ |
| H A D | kernel_mode_vector.c | 147 uvstate = ¤t->thread.vstate; in riscv_v_start_kernel_context()
171 struct __riscv_v_ext_state *vstate = ¤t->thread.kernel_vstate; in riscv_v_context_nesting_end() local
183 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_context_nesting_end()
218 riscv_v_vstate_save(¤t->thread.vstate, task_pt_regs(current)); in kernel_vector_begin()
|
| H A D | signal.c | 93 riscv_v_vstate_save(¤t->thread.vstate, regs); in save_v_state()
97 err = __copy_to_user(&state->v_state, ¤t->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(¤t->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 D | process.c | 199 kfree(current->thread.vstate.datap); in flush_thread()
200 memset(¤t->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/kernel/bpf/ |
| H A D | log.c | 700 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 D | verifier.c | 3210 struct bpf_verifier_state *vstate = env->cur_state; in check_reg_arg() local
3211 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_reg_arg()
3787 struct bpf_verifier_state *vstate = env->cur_state; in mark_reg_stack_read() local
3788 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_reg_stack_read()
3857 struct bpf_verifier_state *vstate = env->cur_state; in check_stack_read_fixed_off() local
3858 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_stack_read_fixed_off()
4205 struct bpf_verifier_state *vstate = env->cur_state; in check_stack_arg_read() local
4221 caller = vstate->frame[vstate->curframe - 1]; in check_stack_arg_read()
4223 cur = vstate->frame[vstate->curframe]; in check_stack_arg_read()
6587 struct bpf_verifier_state *vstate = env->cur_state; in check_load_mem() local
[all …]
|
| H A D | diagnostics.c | 1551 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/tools/perf/util/ |
| H A D | pmus.c | 593 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 D | bpf_verifier.h | 1471 void print_verifier_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate,
1473 void print_insn_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate,
|
| /linux/net/netfilter/ |
| H A D | nf_tables_api.c | 141 if (chain->vstate.depth >= ctx->level && in nft_chain_vstate_valid()
142 chain->vstate.hook_mask[type] & BIT(hooknum)) in nft_chain_vstate_valid()
4151 memset(&chain->vstate, 0, sizeof(chain->vstate)); in nft_chain_vstate_update()
4161 chain->vstate.hook_mask[type] |= BIT(hooknum); in nft_chain_vstate_update()
4162 if (chain->vstate.depth < ctx->level) in nft_chain_vstate_update()
4163 chain->vstate.depth = ctx->level; in nft_chain_vstate_update()
4242 memset(&chain->vstate, 0, sizeof(chain->vstate)); in nft_table_validate()
|
| /linux/include/net/netfilter/ |
| H A D | nf_tables.h | 1155 struct nft_chain_validate_state vstate; member
|