23 	WRITE_ONCE(current->thread.riscv_v_flags, flags);  in riscv_v_flags_set()
86 	return &current->thread.riscv_v_flags;  in riscv_v_flags_ptr()
116 	if (riscv_v_ctx_get_depth() != 0 || !riscv_preempt_v_started(current))  in riscv_v_stop_kernel_context()
119 	riscv_preempt_v_clear_dirty(current);  in riscv_v_stop_kernel_context()
128 	kvstate = &current->thread.kernel_vstate;  in riscv_v_start_kernel_context()
132 	if (riscv_preempt_v_started(current)) {  in riscv_v_start_kernel_context()
136 		if (riscv_preempt_v_dirty(current)) {  in riscv_v_start_kernel_context()
138 			riscv_preempt_v_clear_dirty(current);  in riscv_v_start_kernel_context()
140 		riscv_preempt_v_set_restore(current);  in riscv_v_start_kernel_context()
146 	if ((task_pt_regs(current)->status & SR_VS) == SR_VS_DIRTY) {  in riscv_v_start_kernel_context()
147 		uvstate = &current->thread.vstate;  in riscv_v_start_kernel_context()
150 	riscv_preempt_v_clear_dirty(current);  in riscv_v_start_kernel_context()
159 	if (!riscv_preempt_v_started(current))  in riscv_v_context_nesting_start()
171 	struct __riscv_v_ext_state *vstate = &current->thread.kernel_vstate;  in riscv_v_context_nesting_end()
176 	if (!riscv_preempt_v_started(current))  in riscv_v_context_nesting_end()
182 		if (riscv_preempt_v_restore(current)) {  in riscv_v_context_nesting_end()
218 		riscv_v_vstate_save(&current->thread.vstate, task_pt_regs(current));  in kernel_vector_begin()
222 		riscv_v_vstate_set_restore(current, task_pt_regs(current));  in kernel_vector_begin()
229  * kernel_vector_end(): give the CPU vector registers back to the current task