Home
last modified time | relevance | path

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

/linux-6.15/arch/riscv/kernel/
H A Dptrace.c95 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_get() local
111 ptrace_vstate.vstart = vstate->vstart; in riscv_vr_get()
112 ptrace_vstate.vl = vstate->vl; in riscv_vr_get()
113 ptrace_vstate.vtype = vstate->vtype; in riscv_vr_get()
114 ptrace_vstate.vcsr = vstate->vcsr; in riscv_vr_get()
115 ptrace_vstate.vlenb = vstate->vlenb; in riscv_vr_get()
130 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_set() local
145 vstate->vstart = ptrace_vstate.vstart; in riscv_vr_set()
146 vstate->vl = ptrace_vstate.vl; in riscv_vr_set()
147 vstate->vtype = ptrace_vstate.vtype; in riscv_vr_set()
[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 Dvector.c135 if (tsk->thread.vstate.datap) in riscv_v_thread_free()
136 kmem_cache_free(riscv_v_user_cachep, tsk->thread.vstate.datap); in riscv_v_thread_free()
208 WARN_ON(current->thread.vstate.datap); in riscv_v_first_use_handler()
215 if (riscv_v_thread_zalloc(riscv_v_user_cachep, &current->thread.vstate)) { in riscv_v_first_use_handler()
H A Dsignal.c90 riscv_v_vstate_save(&current->thread.vstate, regs); in save_v_state()
94 err = __copy_to_user(&state->v_state, &current->thread.vstate, in save_v_state()
99 err |= __copy_to_user(datap, current->thread.vstate.datap, riscv_v_vsize); in save_v_state()
130 err = __copy_from_user(&current->thread.vstate, &state->v_state, in __restore_v_state()
143 return copy_from_user(current->thread.vstate.datap, datap, riscv_v_vsize); in __restore_v_state()
H A Dprocess.c180 kfree(current->thread.vstate.datap); in flush_thread()
181 memset(&current->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in flush_thread()
202 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
/linux-6.15/arch/riscv/include/asm/
H A Dvector.h300 static inline void riscv_v_vstate_save(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_save() argument
304 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save()
309 static inline void riscv_v_vstate_restore(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_restore() argument
313 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore()
376 riscv_v_vstate_save(&prev->thread.vstate, regs); in __switch_to_vector()
402 #define riscv_v_vstate_save(vstate, regs) do {} while (0) argument
403 #define riscv_v_vstate_restore(vstate, regs) do {} while (0) argument
H A Dentry-common.h19 riscv_v_vstate_restore(&current->thread.vstate, regs); in arch_exit_to_user_mode_prepare()
H A Dprocessor.h108 struct __riscv_v_ext_state vstate; member
/linux-6.15/kernel/bpf/
H A Dlog.c757 void print_verifier_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate, in print_verifier_state() argument
760 const struct bpf_func_state *state = vstate->frame[frameno]; in print_verifier_state()
848 if (vstate->acquired_refs && vstate->refs[0].id) { in print_verifier_state()
849 verbose(env, " refs=%d", vstate->refs[0].id); in print_verifier_state()
850 for (i = 1; i < vstate->acquired_refs; i++) in print_verifier_state()
851 if (vstate->refs[i].id) in print_verifier_state()
852 verbose(env, ",%d", vstate->refs[i].id); in print_verifier_state()
869 void print_insn_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate, in print_insn_state() argument
879 print_verifier_state(env, vstate, frameno, false); in print_insn_state()
H A Dverifier.c3740 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_reg_arg()
5264 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_reg_stack_read()
5305 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_stack_read_fixed_off()
5633 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_mem_region_access()
5963 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_map_access()
10184 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_pkt_end()
14287 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in adjust_ptr_min_max_vals()
15181 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in adjust_reg_min_max_vals()
15262 print_verifier_state(env, vstate, vstate->curframe, true); in adjust_reg_min_max_vals()
15267 print_verifier_state(env, vstate, vstate->curframe, true); in adjust_reg_min_max_vals()
[all …]
/linux-6.15/include/linux/
H A Dbpf_verifier.h1015 void print_verifier_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate,
1017 void print_insn_state(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate,
/linux-6.15/tools/perf/util/
H A Dpmus.c476 static int perf_pmus__print_pmu_events__callback(void *vstate, in perf_pmus__print_pmu_events__callback() argument
479 struct events_callback_state *state = vstate; in perf_pmus__print_pmu_events__callback()
/linux-6.15/drivers/gpu/drm/amd/pm/
H A Damdgpu_dpm.c968 struct amd_vce_state *vstate = NULL; in amdgpu_dpm_get_vce_clock_state() local
974 vstate = pp_funcs->get_vce_clock_state(adev->powerplay.pp_handle, in amdgpu_dpm_get_vce_clock_state()
978 return vstate; in amdgpu_dpm_get_vce_clock_state()