0f4b825797
This patch adds vector context save/restore for guest VCPUs. To reduce the impact on KVM performance, the implementation imitates the FP context switch mechanism to lazily store and restore the vector context only when the kernel enters/exits the in-kernel run loop and not during the KVM world switch. Signed-off-by: Vincent Chen <vincent.chen@sifive.com> Signed-off-by: Greentime Hu <greentime.hu@sifive.com> Signed-off-by: Andy Chiu <andy.chiu@sifive.com> Reviewed-by: Anup Patel <anup@brainfault.org> Acked-by: Anup Patel <anup@brainfault.org> Link: https://lore.kernel.org/r/20230605110724.21391-20-andy.chiu@sifive.com Signed-off-by: Palmer Dabbelt <palmer@rivosinc.com>
83 lines
2.2 KiB
C
83 lines
2.2 KiB
C
/* SPDX-License-Identifier: GPL-2.0-only */
|
|
/*
|
|
* Copyright (C) 2022 SiFive
|
|
*
|
|
* Authors:
|
|
* Vincent Chen <vincent.chen@sifive.com>
|
|
* Greentime Hu <greentime.hu@sifive.com>
|
|
*/
|
|
|
|
#ifndef __KVM_VCPU_RISCV_VECTOR_H
|
|
#define __KVM_VCPU_RISCV_VECTOR_H
|
|
|
|
#include <linux/types.h>
|
|
|
|
#ifdef CONFIG_RISCV_ISA_V
|
|
#include <asm/vector.h>
|
|
#include <asm/kvm_host.h>
|
|
|
|
static __always_inline void __kvm_riscv_vector_save(struct kvm_cpu_context *context)
|
|
{
|
|
__riscv_v_vstate_save(&context->vector, context->vector.datap);
|
|
}
|
|
|
|
static __always_inline void __kvm_riscv_vector_restore(struct kvm_cpu_context *context)
|
|
{
|
|
__riscv_v_vstate_restore(&context->vector, context->vector.datap);
|
|
}
|
|
|
|
void kvm_riscv_vcpu_vector_reset(struct kvm_vcpu *vcpu);
|
|
void kvm_riscv_vcpu_guest_vector_save(struct kvm_cpu_context *cntx,
|
|
unsigned long *isa);
|
|
void kvm_riscv_vcpu_guest_vector_restore(struct kvm_cpu_context *cntx,
|
|
unsigned long *isa);
|
|
void kvm_riscv_vcpu_host_vector_save(struct kvm_cpu_context *cntx);
|
|
void kvm_riscv_vcpu_host_vector_restore(struct kvm_cpu_context *cntx);
|
|
int kvm_riscv_vcpu_alloc_vector_context(struct kvm_vcpu *vcpu,
|
|
struct kvm_cpu_context *cntx);
|
|
void kvm_riscv_vcpu_free_vector_context(struct kvm_vcpu *vcpu);
|
|
#else
|
|
|
|
struct kvm_cpu_context;
|
|
|
|
static inline void kvm_riscv_vcpu_vector_reset(struct kvm_vcpu *vcpu)
|
|
{
|
|
}
|
|
|
|
static inline void kvm_riscv_vcpu_guest_vector_save(struct kvm_cpu_context *cntx,
|
|
unsigned long *isa)
|
|
{
|
|
}
|
|
|
|
static inline void kvm_riscv_vcpu_guest_vector_restore(struct kvm_cpu_context *cntx,
|
|
unsigned long *isa)
|
|
{
|
|
}
|
|
|
|
static inline void kvm_riscv_vcpu_host_vector_save(struct kvm_cpu_context *cntx)
|
|
{
|
|
}
|
|
|
|
static inline void kvm_riscv_vcpu_host_vector_restore(struct kvm_cpu_context *cntx)
|
|
{
|
|
}
|
|
|
|
static inline int kvm_riscv_vcpu_alloc_vector_context(struct kvm_vcpu *vcpu,
|
|
struct kvm_cpu_context *cntx)
|
|
{
|
|
return 0;
|
|
}
|
|
|
|
static inline void kvm_riscv_vcpu_free_vector_context(struct kvm_vcpu *vcpu)
|
|
{
|
|
}
|
|
#endif
|
|
|
|
int kvm_riscv_vcpu_get_reg_vector(struct kvm_vcpu *vcpu,
|
|
const struct kvm_one_reg *reg,
|
|
unsigned long rtype);
|
|
int kvm_riscv_vcpu_set_reg_vector(struct kvm_vcpu *vcpu,
|
|
const struct kvm_one_reg *reg,
|
|
unsigned long rtype);
|
|
#endif
|