/linux-master/arch/riscv/kernel/ |
H A D | ptrace.c | 92 struct __riscv_v_ext_state *vstate = &target->thread.vstate; local 104 riscv_v_vstate_save(¤t->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 D | kernel_mode_vector.c | 147 uvstate = ¤t->thread.vstate; 171 struct __riscv_v_ext_state *vstate = ¤t->thread.kernel_vstate; local 183 __riscv_v_vstate_restore(vstate, vstate->datap); 218 riscv_v_vstate_save(¤t->thread.vstate, task_pt_regs(current));
|
H A D | vector.c | 125 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, ¤t->thread.vstate)) {
|
H A D | process.c | 170 kfree(current->thread.vstate.datap); 171 memset(¤t->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); 188 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state));
|
H A D | signal.c | 90 riscv_v_vstate_save(¤t->thread.vstate, regs); 93 /* Copy everything of vstate but datap. */ 94 err = __copy_to_user(&state->v_state, ¤t->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(¤t->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 D | entry-common.h | 19 riscv_v_vstate_restore(¤t->thread.vstate, regs);
|
H A D | vector.h | 177 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 D | processor.h | 122 struct __riscv_v_ext_state vstate; member in struct:thread_struct
|
/linux-master/tools/perf/util/ |
H A D | pmus.c | 412 static int perf_pmus__print_pmu_events__callback(void *vstate, argument 415 struct events_callback_state *state = vstate;
|
/linux-master/kernel/bpf/ |
H A D | verifier.c | 3292 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 D | amdgpu_dpm.c | 896 struct amd_vce_state *vstate = NULL; local 902 vstate = pp_funcs->get_vce_clock_state(adev->powerplay.pp_handle, 906 return vstate;
|