Home
last modified time | relevance | path

Searched refs:__riscv_v_ext_state (Results 1 – 8 of 8) sorted by relevance

/linux/arch/riscv/include/asm/
H A Dvector.h129 static __always_inline void __vstate_csr_save(struct __riscv_v_ext_state *dest) in __vstate_csr_save()
167 static __always_inline void __vstate_csr_restore(struct __riscv_v_ext_state *src) in __vstate_csr_restore()
196 static inline void __riscv_v_vstate_save(struct __riscv_v_ext_state *save_to, in __riscv_v_vstate_save()
233 static inline void __riscv_v_vstate_restore(struct __riscv_v_ext_state *restore_from, in __riscv_v_vstate_restore()
306 static inline void riscv_v_vstate_save(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_save()
315 static inline void riscv_v_vstate_restore(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_restore()
H A Dprocessor.h117 struct __riscv_v_ext_state vstate;
119 struct __riscv_v_ext_state kernel_vstate;
/linux/arch/riscv/kernel/
H A Dkernel_mode_vector.c126 struct __riscv_v_ext_state *kvstate, *uvstate; in riscv_v_start_kernel_context()
171 struct __riscv_v_ext_state *vstate = &current->thread.kernel_vstate; in riscv_v_context_nesting_end()
H A Dprocess.c200 memset(&current->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in flush_thread()
221 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
222 memset(&dst->thread.kernel_vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
H A Dptrace.c99 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_get()
131 static int invalid_ptrace_v_csr(struct __riscv_v_ext_state *vstate, in invalid_ptrace_v_csr()
223 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_set()
H A Dsignal.c98 offsetof(struct __riscv_v_ext_state, datap)); in save_v_state()
130 offsetof(struct __riscv_v_ext_state, datap)); in __restore_v_state()
/linux/tools/testing/selftests/riscv/sigreturn/
H A Dsigreturn.c26 struct __riscv_v_ext_state *v_ext_state; in vector_override()
/linux/arch/riscv/include/uapi/asm/
H A Dptrace.h101 struct __riscv_v_ext_state { struct