Lines Matching refs:SR_VS
45 regs->status = (regs->status & ~SR_VS) | SR_VS_CLEAN; in __riscv_v_vstate_clean()
50 regs->status = (regs->status & ~SR_VS) | SR_VS_DIRTY; in __riscv_v_vstate_dirty()
55 regs->status = (regs->status & ~SR_VS) | SR_VS_OFF; in riscv_v_vstate_off()
60 regs->status = (regs->status & ~SR_VS) | SR_VS_INITIAL; in riscv_v_vstate_on()
65 return (regs->status & SR_VS) != 0; in riscv_v_vstate_query()
70 csr_set(CSR_SSTATUS, SR_VS); in riscv_v_enable()
75 csr_clear(CSR_SSTATUS, SR_VS); in riscv_v_disable()
170 if ((regs->status & SR_VS) == SR_VS_OFF) in riscv_v_vstate_discard()
180 if ((regs->status & SR_VS) == SR_VS_DIRTY) { in riscv_v_vstate_save()
189 if ((regs->status & SR_VS) != SR_VS_OFF) { in riscv_v_vstate_restore()
198 if ((regs->status & SR_VS) != SR_VS_OFF) { in riscv_v_vstate_set_restore()