ARM: Use type override hacks only in NEON code

[PATCH 0/2] ARM: Use type override hacks only in NEON code

Posted by Ard Biesheuvel 2 weeks, 2 days ago

From: Ard Biesheuvel <ardb@kernel.org>

Now that the RAID-6 code can no longer be built for user space, we can
drop the direct dependency on the arm_neon.h system header, and include
asm/neon-intrinsics.h instead.

Since asm/neon-intrinsics.h has all the type overrides needed to include
arm_neon.h without conflicts in the uintXX_t types, those hacks can be
dropped from asm/types.h, and so the file can be dropped entirely.

Cc: Eric Biggers <ebiggers@kernel.org>
Cc: Christoph Hellwig <hch@lst.de>
Cc: Russell King <linux@armlinux.org.uk>
Cc: Arnd Bergmann <arnd@arndb.de>

Ard Biesheuvel (2):
  lib/raid6: Switch to Linux's NEON intrinsics header
  ARM: Remove hacked-up asm/types.h header

 arch/arm/include/uapi/asm/types.h     | 41 --------------------
 lib/raid/raid6/arm/neon.uc            |  2 +-
 lib/raid/raid6/arm/recov_neon_inner.c |  2 +-
 3 files changed, 2 insertions(+), 43 deletions(-)
 delete mode 100644 arch/arm/include/uapi/asm/types.h

-- 
2.55.0.1003.g10538fe699-goog

Re: [PATCH 0/2] ARM: Use type override hacks only in NEON code

Posted by Eric Biggers 1 week ago

On Wed, Sep 09, 2026 at 06:33:20PM +0200, Ard Biesheuvel wrote:
> From: Ard Biesheuvel <ardb@kernel.org>
> 
> Now that the RAID-6 code can no longer be built for user space, we can
> drop the direct dependency on the arm_neon.h system header, and include
> asm/neon-intrinsics.h instead.
> 
> Since asm/neon-intrinsics.h has all the type overrides needed to include
> arm_neon.h without conflicts in the uintXX_t types, those hacks can be
> dropped from asm/types.h, and so the file can be dropped entirely.
> 
> Cc: Eric Biggers <ebiggers@kernel.org>
> Cc: Christoph Hellwig <hch@lst.de>
> Cc: Russell King <linux@armlinux.org.uk>
> Cc: Arnd Bergmann <arnd@arndb.de>
> 
> Ard Biesheuvel (2):
>   lib/raid6: Switch to Linux's NEON intrinsics header
>   ARM: Remove hacked-up asm/types.h header

Reviewed-by: Eric Biggers <ebiggers@kernel.org>

- Eric

Re: [PATCH 0/2] ARM: Use type override hacks only in NEON code

Posted by Ard Biesheuvel 1 week ago

On Fri, 18 Sep 2026, at 04:30, Eric Biggers wrote:
> On Wed, Sep 09, 2026 at 06:33:20PM +0200, Ard Biesheuvel wrote:
>> From: Ard Biesheuvel <ardb@kernel.org>
>> 
>> Now that the RAID-6 code can no longer be built for user space, we can
>> drop the direct dependency on the arm_neon.h system header, and include
>> asm/neon-intrinsics.h instead.
>> 
>> Since asm/neon-intrinsics.h has all the type overrides needed to include
>> arm_neon.h without conflicts in the uintXX_t types, those hacks can be
>> dropped from asm/types.h, and so the file can be dropped entirely.
>> 
>> Cc: Eric Biggers <ebiggers@kernel.org>
>> Cc: Christoph Hellwig <hch@lst.de>
>> Cc: Russell King <linux@armlinux.org.uk>
>> Cc: Arnd Bergmann <arnd@arndb.de>
>> 
>> Ard Biesheuvel (2):
>>   lib/raid6: Switch to Linux's NEON intrinsics header
>>   ARM: Remove hacked-up asm/types.h header
>
> Reviewed-by: Eric Biggers <ebiggers@kernel.org>
>

Thanks.

I've dropped these into rmk's patch tracker.