Searched refs:vstate (Results 1 - 11 of 11) sorted by relevance

/linux-master/arch/riscv/kernel/
H A Dptrace.c92 struct __riscv_v_ext_state *vstate = &target->thread.vstate; local
104 riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current));
108 ptrace_vstate.vstart = vstate->vstart;
109 ptrace_vstate.vl = vstate->vl;
110 ptrace_vstate.vtype = vstate->vtype;
111 ptrace_vstate.vcsr = vstate->vcsr;
112 ptrace_vstate.vlenb = vstate->vlenb;
114 /* Copy vector header from vstate. */
117 /* Copy all the vector registers from vstate
127 struct __riscv_v_ext_state *vstate = &target->thread.vstate; local
[all...]
H A Dkernel_mode_vector.c147 uvstate = &current->thread.vstate;
171 struct __riscv_v_ext_state *vstate = &current->thread.kernel_vstate; local
183 __riscv_v_vstate_restore(vstate, vstate->datap);
218 riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current));
H A Dvector.c125 if (tsk->thread.vstate.datap)
126 kmem_cache_free(riscv_v_user_cachep, tsk->thread.vstate.datap);
195 WARN_ON(current->thread.vstate.datap);
202 if (riscv_v_thread_zalloc(riscv_v_user_cachep, &current->thread.vstate)) {
H A Dprocess.c170 kfree(current->thread.vstate.datap);
171 memset(&current->thread.vstate, 0, sizeof(struct __riscv_v_ext_state));
188 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state));
H A Dsignal.c90 riscv_v_vstate_save(&current->thread.vstate, regs);
93 /* Copy everything of vstate but datap. */
94 err = __copy_to_user(&state->v_state, &current->thread.vstate,
99 err |= __copy_to_user(datap, current->thread.vstate.datap, riscv_v_vsize);
123 * Mark the vstate as clean prior performing the actual copy,
124 * to avoid getting the vstate incorrectly clobbered by the
130 err = __copy_from_user(&current->thread.vstate, &state->v_state,
143 return copy_from_user(current->thread.vstate.datap, datap, riscv_v_vsize);
/linux-master/arch/riscv/include/asm/
H A Dentry-common.h19 riscv_v_vstate_restore(&current->thread.vstate, regs);
H A Dvector.h177 static inline void riscv_v_vstate_save(struct __riscv_v_ext_state *vstate, argument
181 __riscv_v_vstate_save(vstate, vstate->datap);
186 static inline void riscv_v_vstate_restore(struct __riscv_v_ext_state *vstate, argument
190 __riscv_v_vstate_restore(vstate, vstate->datap);
253 riscv_v_vstate_save(&prev->thread.vstate, regs);
276 #define riscv_v_vstate_save(vstate, regs) do {} while (0)
277 #define riscv_v_vstate_restore(vstate, regs) do {} while (0)
H A Dprocessor.h122 struct __riscv_v_ext_state vstate; member in struct:thread_struct
/linux-master/tools/perf/util/
H A Dpmus.c412 static int perf_pmus__print_pmu_events__callback(void *vstate, argument
415 struct events_callback_state *state = vstate;
/linux-master/kernel/bpf/
H A Dverifier.c3292 struct bpf_verifier_state *vstate = env->cur_state; local
3293 struct bpf_func_state *state = vstate->frame[vstate->curframe];
4743 struct bpf_verifier_state *vstate = env->cur_state; local
4744 struct bpf_func_state *state = vstate->frame[vstate->curframe];
4784 struct bpf_verifier_state *vstate = env->cur_state; local
4785 struct bpf_func_state *state = vstate->frame[vstate->curframe];
5110 struct bpf_verifier_state *vstate local
5414 struct bpf_verifier_state *vstate = env->cur_state; local
9222 mark_pkt_end(struct bpf_verifier_state *vstate, int regn, bool range_open) argument
12696 struct bpf_verifier_state *vstate = env->cur_state; local
12785 struct bpf_verifier_state *vstate = env->cur_state; local
12911 struct bpf_verifier_state *vstate = env->cur_state; local
13878 struct bpf_verifier_state *vstate = env->cur_state; local
14215 find_good_pkt_pointers(struct bpf_verifier_state *vstate, struct bpf_reg_state *dst_reg, enum bpf_reg_type type, bool range_right_open) argument
14812 mark_ptr_or_null_regs(struct bpf_verifier_state *vstate, u32 regno, bool is_null) argument
14937 find_equal_scalars(struct bpf_verifier_state *vstate, struct bpf_reg_state *known_reg) argument
16955 propagate_liveness(struct bpf_verifier_env *env, const struct bpf_verifier_state *vstate, struct bpf_verifier_state *vparent) argument
[all...]
/linux-master/drivers/gpu/drm/amd/pm/
H A Damdgpu_dpm.c896 struct amd_vce_state *vstate = NULL; local
902 vstate = pp_funcs->get_vce_clock_state(adev->powerplay.pp_handle,
906 return vstate;

Completed in 351 milliseconds