1 /* SPDX-License-Identifier: GPL-2.0-only */ 2 /* 3 * Copyright (C) 2022 SiFive 4 * 5 * Authors: 6 * Vincent Chen <vincent.chen@sifive.com> 7 * Greentime Hu <greentime.hu@sifive.com> 8 */ 9 10 #ifndef __KVM_VCPU_RISCV_VECTOR_H 11 #define __KVM_VCPU_RISCV_VECTOR_H 12 13 #include <linux/types.h> 14 15 #ifdef CONFIG_RISCV_ISA_V 16 #include <asm/vector.h> 17 #include <asm/kvm_host.h> 18 19 static __always_inline void __kvm_riscv_vector_save(struct kvm_cpu_context *context) 20 { 21 __riscv_v_vstate_save(&context->vector, context->vector.datap); 22 } 23 24 static __always_inline void __kvm_riscv_vector_restore(struct kvm_cpu_context *context) 25 { 26 __riscv_v_vstate_restore(&context->vector, context->vector.datap); 27 } 28 29 void kvm_riscv_vcpu_vector_reset(struct kvm_vcpu *vcpu); 30 void kvm_riscv_vcpu_guest_vector_save(struct kvm_cpu_context *cntx, 31 unsigned long *isa); 32 void kvm_riscv_vcpu_guest_vector_restore(struct kvm_cpu_context *cntx, 33 unsigned long *isa); 34 void kvm_riscv_vcpu_host_vector_save(struct kvm_cpu_context *cntx); 35 void kvm_riscv_vcpu_host_vector_restore(struct kvm_cpu_context *cntx); 36 int kvm_riscv_vcpu_alloc_vector_context(struct kvm_vcpu *vcpu, 37 struct kvm_cpu_context *cntx); 38 void kvm_riscv_vcpu_free_vector_context(struct kvm_vcpu *vcpu); 39 #else 40 41 struct kvm_cpu_context; 42 43 static inline void kvm_riscv_vcpu_vector_reset(struct kvm_vcpu *vcpu) 44 { 45 } 46 47 static inline void kvm_riscv_vcpu_guest_vector_save(struct kvm_cpu_context *cntx, 48 unsigned long *isa) 49 { 50 } 51 52 static inline void kvm_riscv_vcpu_guest_vector_restore(struct kvm_cpu_context *cntx, 53 unsigned long *isa) 54 { 55 } 56 57 static inline void kvm_riscv_vcpu_host_vector_save(struct kvm_cpu_context *cntx) 58 { 59 } 60 61 static inline void kvm_riscv_vcpu_host_vector_restore(struct kvm_cpu_context *cntx) 62 { 63 } 64 65 static inline int kvm_riscv_vcpu_alloc_vector_context(struct kvm_vcpu *vcpu, 66 struct kvm_cpu_context *cntx) 67 { 68 return 0; 69 } 70 71 static inline void kvm_riscv_vcpu_free_vector_context(struct kvm_vcpu *vcpu) 72 { 73 } 74 #endif 75 76 int kvm_riscv_vcpu_get_reg_vector(struct kvm_vcpu *vcpu, 77 const struct kvm_one_reg *reg); 78 int kvm_riscv_vcpu_set_reg_vector(struct kvm_vcpu *vcpu, 79 const struct kvm_one_reg *reg); 80 #endif 81