Home
last modified time | relevance | path

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

/linux/arch/riscv/kernel/
H A Dkernel_mode_vector.c146 if ((task_pt_regs(current)->status & SR_VS) == SR_VS_DIRTY) { in riscv_v_start_kernel_context()
163 if (depth == 0 && (regs->status & SR_VS) == SR_VS_DIRTY) in riscv_v_context_nesting_start()
/linux/arch/riscv/include/asm/
H A Dvector.h50 regs->status = (regs->status & ~SR_VS) | SR_VS_DIRTY; in __riscv_v_vstate_dirty()
180 if ((regs->status & SR_VS) == SR_VS_DIRTY) { in riscv_v_vstate_save()
H A Dcsr.h31 #define SR_VS_DIRTY _AC(0x00000600, UL) macro
/linux/arch/riscv/kvm/
H A Dvcpu_vector.c43 if ((cntx->sstatus & SR_VS) == SR_VS_DIRTY) { in kvm_riscv_vcpu_guest_vector_save()
/linux/tools/arch/riscv/include/asm/
H A Dcsr.h30 #define SR_VS_DIRTY _AC(0x00000600, UL) macro