Searched refs:kernel_vstate (Results 1 – 6 of 6) sorted by relevance
119 riscv_v_thread_zalloc(riscv_v_kernel_cachep, &tsk->thread.kernel_vstate); in riscv_v_thread_alloc()128 if (tsk->thread.kernel_vstate.datap) in riscv_v_thread_free()129 kmem_cache_free(riscv_v_kernel_cachep, tsk->thread.kernel_vstate.datap); in riscv_v_thread_free()
128 kvstate = ¤t->thread.kernel_vstate; in riscv_v_start_kernel_context()171 struct __riscv_v_ext_state *vstate = ¤t->thread.kernel_vstate; in riscv_v_context_nesting_end()
198 memset(&dst->thread.kernel_vstate, 0, sizeof(struct __riscv_v_ext_state)); in arch_dup_task_struct()
43 if (IS_ENABLED(CONFIG_RISCV_ISA_V_PREEMPTIVE) && current->thread.kernel_vstate.datap) { in may_use_simd()
247 __riscv_v_vstate_save(&prev->thread.kernel_vstate, in __switch_to_vector()248 prev->thread.kernel_vstate.datap); in __switch_to_vector()
109 struct __riscv_v_ext_state kernel_vstate; member