Received-SPF: pass (google.com: domain of linux-kernel-owner@vger.kernel.org designates 2620:137:e000::1:20 as permitted sender) client-ip=2620:137:e000::1:20;
Date:   Mon, 3 Jul 2023 10:54:22 +1000
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>,
        Palmer Dabbelt <palmer@rivosinc.com>,
        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
Message-ID: <20230703105422.06713241@canb.auug.org.au>
In-Reply-To: <20230619123300.389e3dc9@canb.auug.org.au>
References: <20230619123300.389e3dc9@canb.auug.org.au>
MIME-Version: 1.0
Content-Type: multipart/signed; boundary="Sig_/N0PlDi_uGULgrk/j+l8HVmW";
 protocol="application/pgp-signature"; micalg=pgp-sha256
Precedence: bulk

--Sig_/N0PlDi_uGULgrk/j+l8HVmW
Content-Type: text/plain; charset=US-ASCII
Content-Transfer-Encoding: quoted-printable

Hi all,

On Mon, 19 Jun 2023 12:33:00 +1000 Stephen Rothwell <sfr@canb.auug.org.au> =
wrote:
>
> Today's linux-next merge of the kvm-riscv tree got a conflict in:
>=20
>   arch/riscv/include/uapi/asm/kvm.h
>=20
> between commit:
>=20
>   0f4b82579716 ("riscv: KVM: Add vector lazy save/restore support")
>=20
> from the risc-v tree and commits:
>=20
>   00f918f61c56 ("RISC-V: KVM: Skeletal in-kernel AIA irqchip support")
>   89d01306e34d ("RISC-V: KVM: Implement device interface for AIA irqchip")
>   289a007b98b0 ("RISC-V: KVM: Expose APLIC registers as attributes of AIA=
 irqchip")
>   4fe9eadad83b ("RISC-V: KVM: Expose IMSIC registers as attributes of AIA=
 irqchip")
>=20
> from the kvm-riscv tree.
>=20
> 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.
>=20
>=20
> diff --cc arch/riscv/include/uapi/asm/kvm.h
> index 855c047e86d4,61d7fecc4899..000000000000
> --- a/arch/riscv/include/uapi/asm/kvm.h
> +++ b/arch/riscv/include/uapi/asm/kvm.h
> @@@ -204,13 -204,77 +205,84 @@@ enum KVM_RISCV_SBI_EXT_ID=20
>   #define KVM_REG_RISCV_SBI_MULTI_REG_LAST	\
>   		KVM_REG_RISCV_SBI_MULTI_REG(KVM_RISCV_SBI_EXT_MAX - 1)
>  =20
>  +/* 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
> +=20
> + #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
> +=20
> + /*
> +  * 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 wh=
enever
> +  *    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
> +=20
> + #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
> +=20
> + #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)
> +=20
> + #define KVM_DEV_RISCV_AIA_GRP_CTRL		2
> + #define KVM_DEV_RISCV_AIA_CTRL_INIT		0
> +=20
> + /*
> +  * 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
> +=20
> + /*
> +  * The lower 12-bits of the device attribute type contains the iselect
> +  * value of the IMSIC register (range 0x70-0xFF) whereas the higher ord=
er
> +  * 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)
> +=20
> + /* One single KVM irqchip, ie. the AIA */
> + #define KVM_NR_IRQCHIPS			1
> +=20
>   #endif
>  =20
>   #endif /* __LINUX_KVM_RISCV_H */

This is now a conflict between the kvm tree and Linus' tree.

--=20
Cheers,
Stephen Rothwell

--Sig_/N0PlDi_uGULgrk/j+l8HVmW
Content-Type: application/pgp-signature
Content-Description: OpenPGP digital signature

-----BEGIN PGP SIGNATURE-----

iQEzBAEBCAAdFiEENIC96giZ81tWdLgKAVBC80lX0GwFAmSiHD4ACgkQAVBC80lX
0GyDkggAjsX8NQ1Ddpg8RvZ8XzMhPpitacqvVYbaa2qETO8r1QQPqtXMl+lPkHw4
3/5KZNtG3s9N0/BqG4RZkPDvsF+BhNNlLitpqsnJYtmaaC4zd6fxPg4idEPBloid
9TAZuS8hAkA5YGVxjNeA8a+L76IfzFsBzqedA8rfNYCdfiyy+YAcJ2Kyu3XOkWoD
Y9csS8dOtjem0CndS/B/Qr3ih4p9RUxCYhKMxs2qT75gW1Qm37+yCdeM82Ji9Uou
uQbv5ogPlr+LV+J/8WPCZ8rNVhNbbhFz7CevZ8UpGMoWKWlYZclyTAVtvoQIMQbt
6OUvpsXCgU9CjajVWno6EUx3WoWnFg==
=uUkE
-----END PGP SIGNATURE-----

--Sig_/N0PlDi_uGULgrk/j+l8HVmW--