Home
last modified time | relevance | path

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

/openbmc/linux/arch/riscv/kernel/
H A Dptrace.c92 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_get() local
105 ptrace_vstate.vstart = vstate->vstart; in riscv_vr_get()
106 ptrace_vstate.vl = vstate->vl; in riscv_vr_get()
107 ptrace_vstate.vtype = vstate->vtype; in riscv_vr_get()
108 ptrace_vstate.vcsr = vstate->vcsr; in riscv_vr_get()
109 ptrace_vstate.vlenb = vstate->vlenb; in riscv_vr_get()
115 return membuf_write(&to, vstate->datap, riscv_v_vsize); in riscv_vr_get()
124 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_set() local
136 if (vstate->vlenb != ptrace_vstate.vlenb) in riscv_vr_set()
139 vstate->vstart = ptrace_vstate.vstart; in riscv_vr_set()
[all …]
H A Dprocess.c152 kfree(current->thread.vstate.datap); in flush_thread()
153 memset(&current->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in flush_thread()
161 kfree(tsk->thread.vstate.datap); in arch_release_task_struct()
169 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
H A Dvector.c91 current->thread.vstate.datap = datap; in riscv_v_thread_zalloc()
92 memset(&current->thread.vstate, 0, offsetof(struct __riscv_v_ext_state, in riscv_v_thread_zalloc()
158 WARN_ON(current->thread.vstate.datap); in riscv_v_first_use_handler()
H A Dsignal.c90 /* Copy everything of vstate but datap. */ in save_v_state()
91 err = __copy_to_user(&state->v_state, &current->thread.vstate, in save_v_state()
96 err |= __copy_to_user(datap, current->thread.vstate.datap, riscv_v_vsize); in save_v_state()
120 err = __copy_from_user(&current->thread.vstate, &state->v_state, in __restore_v_state()
133 err = copy_from_user(current->thread.vstate.datap, datap, riscv_v_vsize); in __restore_v_state()
/openbmc/linux/arch/riscv/include/asm/
H A Dvector.h169 struct __riscv_v_ext_state *vstate = &task->thread.vstate; in riscv_v_vstate_save() local
171 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save()
180 struct __riscv_v_ext_state *vstate = &task->thread.vstate; in riscv_v_vstate_restore() local
182 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore()
H A Dprocessor.h84 struct __riscv_v_ext_state vstate; member
/openbmc/linux/tools/perf/util/
H A Dpmus.c408 static int perf_pmus__print_pmu_events__callback(void *vstate, in perf_pmus__print_pmu_events__callback() argument
411 struct events_callback_state *state = vstate; in perf_pmus__print_pmu_events__callback()
/openbmc/linux/kernel/bpf/
H A Dverifier.c3394 struct bpf_verifier_state *vstate = env->cur_state; in check_reg_arg() local
3395 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_reg_arg()
4804 struct bpf_verifier_state *vstate = env->cur_state; in mark_reg_stack_read() local
4805 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in mark_reg_stack_read()
4856 struct bpf_verifier_state *vstate = env->cur_state; in check_stack_read_fixed_off() local
4857 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_stack_read_fixed_off()
5154 struct bpf_verifier_state *vstate = env->cur_state; in check_mem_region_access() local
5155 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_mem_region_access()
5410 struct bpf_verifier_state *vstate = env->cur_state; in check_map_access() local
5411 struct bpf_func_state *state = vstate->frame[vstate->curframe]; in check_map_access()
[all …]
/openbmc/linux/drivers/gpu/drm/amd/pm/
H A Damdgpu_dpm.c825 struct amd_vce_state *vstate = NULL; in amdgpu_dpm_get_vce_clock_state() local
831 vstate = pp_funcs->get_vce_clock_state(adev->powerplay.pp_handle, in amdgpu_dpm_get_vce_clock_state()
835 return vstate; in amdgpu_dpm_get_vce_clock_state()