Searched refs:vstate (Results 1 – 11 of 11) sorted by relevance
| /linux/arch/riscv/kernel/ |
| A D | ptrace.c | 92 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_get() local
108 ptrace_vstate.vstart = vstate->vstart; in riscv_vr_get()
109 ptrace_vstate.vl = vstate->vl; in riscv_vr_get()
110 ptrace_vstate.vtype = vstate->vtype; in riscv_vr_get()
111 ptrace_vstate.vcsr = vstate->vcsr; in riscv_vr_get()
112 ptrace_vstate.vlenb = vstate->vlenb; in riscv_vr_get()
127 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_set() local
142 vstate->vstart = ptrace_vstate.vstart; in riscv_vr_set()
143 vstate->vl = ptrace_vstate.vl; in riscv_vr_set()
144 vstate->vtype = ptrace_vstate.vtype; in riscv_vr_set()
[all …]
|
| 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()
|
| A D | vector.c | 125 if (tsk->thread.vstate.datap) in riscv_v_thread_free()
126 kmem_cache_free(riscv_v_user_cachep, tsk->thread.vstate.datap); in riscv_v_thread_free()
198 WARN_ON(current->thread.vstate.datap); in riscv_v_first_use_handler()
205 if (riscv_v_thread_zalloc(riscv_v_user_cachep, ¤t->thread.vstate)) { in riscv_v_first_use_handler()
|
| A D | signal.c | 90 riscv_v_vstate_save(¤t->thread.vstate, regs); in save_v_state()
94 err = __copy_to_user(&state->v_state, ¤t->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(¤t->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()
|
| A D | process.c | 179 kfree(current->thread.vstate.datap); in flush_thread()
180 memset(¤t->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in flush_thread()
197 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
|
| /linux/arch/riscv/include/asm/ |
| A D | vector.h | 177 static inline void riscv_v_vstate_save(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_save() argument
181 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save()
186 static inline void riscv_v_vstate_restore(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_restore() argument
190 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore()
253 riscv_v_vstate_save(&prev->thread.vstate, regs); in __switch_to_vector()
276 #define riscv_v_vstate_save(vstate, regs) do {} while (0) argument
277 #define riscv_v_vstate_restore(vstate, regs) do {} while (0) argument
|
| A D | entry-common.h | 19 riscv_v_vstate_restore(¤t->thread.vstate, regs); in arch_exit_to_user_mode_prepare()
|
| A D | processor.h | 107 struct __riscv_v_ext_state vstate; member
|
| /linux/tools/perf/util/ |
| A D | pmus.c | 427 static int perf_pmus__print_pmu_events__callback(void *vstate, in perf_pmus__print_pmu_events__callback() argument
430 struct events_callback_state *state = vstate; in perf_pmus__print_pmu_events__callback()
|
| /linux/kernel/bpf/ |
| A D | verifier.c | 3368 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_reg_arg()
4881 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_reg_stack_read()
4922 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_stack_read_fixed_off()
5250 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_mem_region_access()
5554 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_map_access()
9445 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_pkt_end()
13060 if (vstate->speculative) in sanitize_ptr_alu()
13139 if (!vstate->speculative) in sanitize_mark_insn_seen()
13259 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in adjust_ptr_min_max_vals()
14161 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in adjust_reg_min_max_vals()
[all …]
|
| /linux/drivers/gpu/drm/amd/pm/ |
| A D | amdgpu_dpm.c | 888 struct amd_vce_state *vstate = NULL; in amdgpu_dpm_get_vce_clock_state() local
894 vstate = pp_funcs->get_vce_clock_state(adev->powerplay.pp_handle, in amdgpu_dpm_get_vce_clock_state()
898 return vstate; in amdgpu_dpm_get_vce_clock_state()
|
Completed in 61 milliseconds