Searched refs:SR_VS (Results 1 – 6 of 6) sorted by relevance
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()[all …]
27 #define SR_VS _AC(0x00000600, UL) /* Vector Status */ macro39 #define SR_FS_VS (SR_FS | SR_VS) /* Vector and Floating-Point Unit */
24 cntx->sstatus &= ~SR_VS; in kvm_riscv_vcpu_vector_reset()36 cntx->sstatus &= ~SR_VS; in kvm_riscv_vcpu_vector_clean()43 if ((cntx->sstatus & SR_VS) == SR_VS_DIRTY) { in kvm_riscv_vcpu_guest_vector_save()53 if ((cntx->sstatus & SR_VS) != SR_VS_OFF) { in kvm_riscv_vcpu_guest_vector_restore()
146 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()
450 li t1, SR_VS
26 #define SR_VS _AC(0x00000600, UL) /* Vector Status */ macro38 #define SR_FS_VS (SR_FS | SR_VS) /* Vector and Floating-Point Unit */