From: Stephen Rothwell <sfr@canb.auug.org.au>
To: Paolo Bonzini <pbonzini@redhat.com>
Cc: Anup Patel <anup@brainfault.org>,
Palmer Dabbelt <palmer@dabbelt.com>,
Paul Walmsley <paul@pwsan.com>, Andy Chiu <andy.chiu@sifive.com>,
Anup Patel <apatel@ventanamicro.com>,
Greentime Hu <greentime.hu@sifive.com>,
Linux Kernel Mailing List <linux-kernel@vger.kernel.org>,
Linux Next Mailing List <linux-next@vger.kernel.org>,
Vincent Chen <vincent.chen@sifive.com>, KVM <kvm@vger.kernel.org>
Subject: Re: linux-next: manual merge of the kvm-riscv tree with the risc-v tree
Date: Mon, 3 Jul 2023 10:55:52 +1000 [thread overview]
Message-ID: <20230703105552.5acf5f9f@canb.auug.org.au> (raw)
In-Reply-To: <20230620124533.45c18fee@canb.auug.org.au>
[-- Attachment #1: Type: text/plain, Size: 4974 bytes --]
Hi all,
On Tue, 20 Jun 2023 12:45:33 +1000 Stephen Rothwell <sfr@canb.auug.org.au> wrote:
>
> Today's linux-next merge of the kvm-riscv tree got a conflict in:
>
> arch/riscv/include/uapi/asm/kvm.h
>
> between commit:
>
> bf78f1ea6e51 ("riscv: kvm: Add V extension to KVM ISA")
>
> from the risc-v tree and commit:
>
> 3177011788ee ("RISC-V: KVM: Allow Svnapot extension for Guest/VM")
>
> from the kvm-riscv tree.
>
> I fixed it up (see below) and can carry the fix as necessary. This
> is now fixed as far as linux-next is concerned, but any non trivial
> conflicts should be mentioned to your upstream maintainer when your tree
> is submitted for merging. You may also want to consider cooperating
> with the maintainer of the conflicting tree to minimise any particularly
> complex conflicts.
>
>
> diff --cc arch/riscv/include/uapi/asm/kvm.h
> index 855c047e86d4,a1ca18408bbd..000000000000
> --- a/arch/riscv/include/uapi/asm/kvm.h
> +++ b/arch/riscv/include/uapi/asm/kvm.h
> @@@ -121,7 -122,7 +122,8 @@@ enum KVM_RISCV_ISA_EXT_ID
> KVM_RISCV_ISA_EXT_ZICBOZ,
> KVM_RISCV_ISA_EXT_ZBB,
> KVM_RISCV_ISA_EXT_SSAIA,
> + KVM_RISCV_ISA_EXT_V,
> + KVM_RISCV_ISA_EXT_SVNAPOT,
> KVM_RISCV_ISA_EXT_MAX,
> };
>
> @@@ -204,13 -205,77 +206,84 @@@ enum KVM_RISCV_SBI_EXT_ID
> #define KVM_REG_RISCV_SBI_MULTI_REG_LAST \
> KVM_REG_RISCV_SBI_MULTI_REG(KVM_RISCV_SBI_EXT_MAX - 1)
>
> +/* V extension registers are mapped as type 9 */
> +#define KVM_REG_RISCV_VECTOR (0x09 << KVM_REG_RISCV_TYPE_SHIFT)
> +#define KVM_REG_RISCV_VECTOR_CSR_REG(name) \
> + (offsetof(struct __riscv_v_ext_state, name) / sizeof(unsigned long))
> +#define KVM_REG_RISCV_VECTOR_REG(n) \
> + ((n) + sizeof(struct __riscv_v_ext_state) / sizeof(unsigned long))
> +
> + /* Device Control API: RISC-V AIA */
> + #define KVM_DEV_RISCV_APLIC_ALIGN 0x1000
> + #define KVM_DEV_RISCV_APLIC_SIZE 0x4000
> + #define KVM_DEV_RISCV_APLIC_MAX_HARTS 0x4000
> + #define KVM_DEV_RISCV_IMSIC_ALIGN 0x1000
> + #define KVM_DEV_RISCV_IMSIC_SIZE 0x1000
> +
> + #define KVM_DEV_RISCV_AIA_GRP_CONFIG 0
> + #define KVM_DEV_RISCV_AIA_CONFIG_MODE 0
> + #define KVM_DEV_RISCV_AIA_CONFIG_IDS 1
> + #define KVM_DEV_RISCV_AIA_CONFIG_SRCS 2
> + #define KVM_DEV_RISCV_AIA_CONFIG_GROUP_BITS 3
> + #define KVM_DEV_RISCV_AIA_CONFIG_GROUP_SHIFT 4
> + #define KVM_DEV_RISCV_AIA_CONFIG_HART_BITS 5
> + #define KVM_DEV_RISCV_AIA_CONFIG_GUEST_BITS 6
> +
> + /*
> + * Modes of RISC-V AIA device:
> + * 1) EMUL (aka Emulation): Trap-n-emulate IMSIC
> + * 2) HWACCEL (aka HW Acceleration): Virtualize IMSIC using IMSIC guest files
> + * 3) AUTO (aka Automatic): Virtualize IMSIC using IMSIC guest files whenever
> + * available otherwise fallback to trap-n-emulation
> + */
> + #define KVM_DEV_RISCV_AIA_MODE_EMUL 0
> + #define KVM_DEV_RISCV_AIA_MODE_HWACCEL 1
> + #define KVM_DEV_RISCV_AIA_MODE_AUTO 2
> +
> + #define KVM_DEV_RISCV_AIA_IDS_MIN 63
> + #define KVM_DEV_RISCV_AIA_IDS_MAX 2048
> + #define KVM_DEV_RISCV_AIA_SRCS_MAX 1024
> + #define KVM_DEV_RISCV_AIA_GROUP_BITS_MAX 8
> + #define KVM_DEV_RISCV_AIA_GROUP_SHIFT_MIN 24
> + #define KVM_DEV_RISCV_AIA_GROUP_SHIFT_MAX 56
> + #define KVM_DEV_RISCV_AIA_HART_BITS_MAX 16
> + #define KVM_DEV_RISCV_AIA_GUEST_BITS_MAX 8
> +
> + #define KVM_DEV_RISCV_AIA_GRP_ADDR 1
> + #define KVM_DEV_RISCV_AIA_ADDR_APLIC 0
> + #define KVM_DEV_RISCV_AIA_ADDR_IMSIC(__vcpu) (1 + (__vcpu))
> + #define KVM_DEV_RISCV_AIA_ADDR_MAX \
> + (1 + KVM_DEV_RISCV_APLIC_MAX_HARTS)
> +
> + #define KVM_DEV_RISCV_AIA_GRP_CTRL 2
> + #define KVM_DEV_RISCV_AIA_CTRL_INIT 0
> +
> + /*
> + * The device attribute type contains the memory mapped offset of the
> + * APLIC register (range 0x0000-0x3FFF) and it must be 4-byte aligned.
> + */
> + #define KVM_DEV_RISCV_AIA_GRP_APLIC 3
> +
> + /*
> + * The lower 12-bits of the device attribute type contains the iselect
> + * value of the IMSIC register (range 0x70-0xFF) whereas the higher order
> + * bits contains the VCPU id.
> + */
> + #define KVM_DEV_RISCV_AIA_GRP_IMSIC 4
> + #define KVM_DEV_RISCV_AIA_IMSIC_ISEL_BITS 12
> + #define KVM_DEV_RISCV_AIA_IMSIC_ISEL_MASK \
> + ((1U << KVM_DEV_RISCV_AIA_IMSIC_ISEL_BITS) - 1)
> + #define KVM_DEV_RISCV_AIA_IMSIC_MKATTR(__vcpu, __isel) \
> + (((__vcpu) << KVM_DEV_RISCV_AIA_IMSIC_ISEL_BITS) | \
> + ((__isel) & KVM_DEV_RISCV_AIA_IMSIC_ISEL_MASK))
> + #define KVM_DEV_RISCV_AIA_IMSIC_GET_ISEL(__attr) \
> + ((__attr) & KVM_DEV_RISCV_AIA_IMSIC_ISEL_MASK)
> + #define KVM_DEV_RISCV_AIA_IMSIC_GET_VCPU(__attr) \
> + ((__attr) >> KVM_DEV_RISCV_AIA_IMSIC_ISEL_BITS)
> +
> + /* One single KVM irqchip, ie. the AIA */
> + #define KVM_NR_IRQCHIPS 1
> +
> #endif
>
> #endif /* __LINUX_KVM_RISCV_H */
This is now a conflict between the kvm tree and Linus' tree.
--
Cheers,
Stephen Rothwell
[-- Attachment #2: OpenPGP digital signature --]
[-- Type: application/pgp-signature, Size: 488 bytes --]
next prev parent reply other threads:[~2023-07-03 0:56 UTC|newest]
Thread overview: 7+ messages / expand[flat|nested] mbox.gz Atom feed top
2023-06-20 2:45 linux-next: manual merge of the kvm-riscv tree with the risc-v tree Stephen Rothwell
2023-07-03 0:55 ` Stephen Rothwell [this message]
-- strict thread matches above, loose matches on Subject: below --
2023-10-30 1:53 Stephen Rothwell
2023-11-01 2:37 ` Stephen Rothwell
2023-11-05 22:31 ` Stephen Rothwell
2023-06-19 2:33 Stephen Rothwell
2023-07-03 0:54 ` Stephen Rothwell
Reply instructions:
You may reply publicly to this message via plain-text email
using any one of the following methods:
* Save the following mbox file, import it into your mail client,
and reply-to-all from there: mbox
Avoid top-posting and favor interleaved quoting:
https://en.wikipedia.org/wiki/Posting_style#Interleaved_style
* Reply using the --to, --cc, and --in-reply-to
switches of git-send-email(1):
git send-email \
--in-reply-to=20230703105552.5acf5f9f@canb.auug.org.au \
--to=sfr@canb.auug.org.au \
--cc=andy.chiu@sifive.com \
--cc=anup@brainfault.org \
--cc=apatel@ventanamicro.com \
--cc=greentime.hu@sifive.com \
--cc=kvm@vger.kernel.org \
--cc=linux-kernel@vger.kernel.org \
--cc=linux-next@vger.kernel.org \
--cc=palmer@dabbelt.com \
--cc=paul@pwsan.com \
--cc=pbonzini@redhat.com \
--cc=vincent.chen@sifive.com \
/path/to/YOUR_REPLY
https://kernel.org/pub/software/scm/git/docs/git-send-email.html
* If your mail client supports setting the In-Reply-To header
via mailto: links, try the mailto: link
Be sure your reply has a Subject: header at the top and a blank line
before the message body.
This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for NNTP newsgroup(s).