Home
last modified time | relevance | path

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

/linux-6.15/arch/riscv/include/asm/
H A Dvector.h123 static __always_inline void __vstate_csr_save(struct __riscv_v_ext_state *dest) in __vstate_csr_save()
161 static __always_inline void __vstate_csr_restore(struct __riscv_v_ext_state *src) in __vstate_csr_restore()
190 static inline void __riscv_v_vstate_save(struct __riscv_v_ext_state *save_to, in __riscv_v_vstate_save()
227 static inline void __riscv_v_vstate_restore(struct __riscv_v_ext_state *restore_from, in __riscv_v_vstate_restore()
300 static inline void riscv_v_vstate_save(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_save()
309 static inline void riscv_v_vstate_restore(struct __riscv_v_ext_state *vstate, in riscv_v_vstate_restore()
H A Dprocessor.h108 struct __riscv_v_ext_state vstate;
110 struct __riscv_v_ext_state kernel_vstate;
H A Dkvm_host.h169 struct __riscv_v_ext_state vector;
/linux-6.15/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.c181 memset(&current->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in flush_thread()
202 memset(&dst->thread.vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
203 memset(&dst->thread.kernel_vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
H A Dvector.c113 struct __riscv_v_ext_state *ctx) in riscv_v_thread_zalloc()
122 memset(ctx, 0, offsetof(struct __riscv_v_ext_state, datap)); in riscv_v_thread_zalloc()
H A Dptrace.c95 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_get()
130 struct __riscv_v_ext_state *vstate = &target->thread.vstate; in riscv_vr_set()
H A Dsignal.c95 offsetof(struct __riscv_v_ext_state, datap)); in save_v_state()
131 offsetof(struct __riscv_v_ext_state, datap)); in __restore_v_state()
/linux-6.15/arch/riscv/include/uapi/asm/
H A Dsigcontext.h21 struct __riscv_v_ext_state v_state;
H A Dkvm.h290 (offsetof(struct __riscv_v_ext_state, name) / sizeof(unsigned long))
292 ((n) + sizeof(struct __riscv_v_ext_state) / sizeof(unsigned long))
H A Dptrace.h100 struct __riscv_v_ext_state { struct
/linux-6.15/tools/testing/selftests/riscv/sigreturn/
H A Dsigreturn.c26 struct __riscv_v_ext_state *v_ext_state; in vector_override()