Home
last modified time | relevance | path

Searched refs:kernel_vstate (Results 1 – 5 of 5) sorted by relevance

/linux/arch/riscv/kernel/
H A Dkernel_mode_vector.c128 kvstate = &current->thread.kernel_vstate; 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.c222 memset(&dst->thread.kernel_vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
/linux/arch/riscv/include/asm/
H A Dsimd.h43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) { in may_use_simd()
H A Dvector.h381 __riscv_v_vstate_save(&prev->thread.kernel_vstate, in __switch_to_vector()
382 prev->thread.kernel_vstate.datap); in __switch_to_vector()
H A Dprocessor.h119 struct __riscv_v_ext_state kernel_vstate; member