97 		regs->t5, regs->t6, get_active_shstk(current));  in __show_regs()
111 	if (!(current->personality & ADDR_NO_RANDOMIZE) && randomize_va_space)  in arch_align_stack()
154 		fstate_restore(current, regs);  in start_thread()
163 	set_shstk_lock(current, false);  in start_thread()
164 	set_shstk_status(current, false);  in start_thread()
165 	set_shstk_base(current, 0, 0);  in start_thread()
166 	set_active_shstk(current, 0);  in start_thread()
171 	set_indir_lp_lock(current, false);  in start_thread()
172 	set_indir_lp_status(current, false);  in start_thread()
192 	fstate_off(current, task_pt_regs(current));  in flush_thread()
193 	memset(&current->thread.fstate, 0, sizeof(current->thread.fstate));  in flush_thread()
197 	riscv_v_vstate_ctrl_init(current);  in flush_thread()
198 	riscv_v_vstate_off(task_pt_regs(current));  in flush_thread()
199 	kfree(current->thread.vstate.datap);  in flush_thread()
200 	memset(&current->thread.vstate, 0, sizeof(struct __riscv_v_ext_state));  in flush_thread()
201 	clear_tsk_thread_flag(current, TIF_RISCV_V_DEFER_RESTORE);  in flush_thread()
205 		envcfg_update_bits(current, ENVCFG_PMM, ENVCFG_PMM_PMLEN_0);  in flush_thread()