Home
last modified time | relevance | path

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

/linux/arch/riscv/kernel/
H A Dptrace.c99 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_get() local
114 riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current)); in riscv_vr_get()
118 ptrace_vstate.vstart = vstate->vstart; in riscv_vr_get()
119 ptrace_vstate.vl = vstate->vl; in riscv_vr_get()
120 ptrace_vstate.vtype = vstate->vtype; in riscv_vr_get()
121 ptrace_vstate.vcsr = vstate->vcsr; in riscv_vr_get()
122 ptrace_vstate.vlenb = vstate->vlenb; in riscv_vr_get()
128 return membuf_write(&to, vstate->datap, riscv_v_vsize); in riscv_vr_get()
131 static int invalid_ptrace_v_csr(struct __riscv_v_ext_state *vstate, in invalid_ptrace_v_csr() argument
139 vlen = vstate->vlenb * 8; in invalid_ptrace_v_csr()
[all …]
H A Dkernel_mode_vector.c147 uvstate = &current->thread.vstate; in riscv_v_start_kernel_context()
171 struct __riscv_v_ext_state *vstate = &current->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(&current->thread.vstate, task_pt_regs(current)); in kernel_vector_begin()
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/arch/riscv/include/asm/
H A Dvector.h306 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
/linux/tools/perf/util/
H A Dpmus.c575 static int perf_pmus__print_pmu_events__callback(void *vstate, in perf_pmus__print_pmu_events__callback() argument
578 struct events_callback_state *state = vstate; in perf_pmus__print_pmu_events__callback()
/linux/kernel/bpf/
H A Dverifier.c3976 struct bpf_verifier_state *vstate = env->cur_state; in check_reg_arg() local
3977 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_reg_arg()
5516 struct bpf_verifier_state *vstate = env->cur_state; in mark_reg_stack_read() local
5517 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_reg_stack_read()
5556 struct bpf_verifier_state *vstate = env->cur_state; in check_stack_read_fixed_off() local
5557 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_stack_read_fixed_off()
5894 struct bpf_verifier_state *vstate = env->cur_state; in check_mem_region_access() local
5895 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_mem_region_access()
6239 struct bpf_verifier_state *vstate = env->cur_state; in check_map_access() local
6240 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_map_access()
[all …]
/linux/net/netfilter/
H A Dnf_tables_api.c143 if (chain->vstate.depth >= ctx->level && in nft_chain_vstate_valid()
144 chain->vstate.hook_mask[type] & BIT(hooknum)) in nft_chain_vstate_valid()
4067 memset(&chain->vstate, 0, sizeof(chain->vstate)); in nft_chain_vstate_update()
4077 chain->vstate.hook_mask[type] |= BIT(hooknum); in nft_chain_vstate_update()
4078 if (chain->vstate.depth < ctx->level) in nft_chain_vstate_update()
4079 chain->vstate.depth = ctx->level; in nft_chain_vstate_update()
4158 memset(&chain->vstate, 0, sizeof(chain->vstate)); in nft_table_validate()
/linux/include/net/netfilter/
H A Dnf_tables.h1160 struct nft_chain_validate_state vstate; member