From ced54ac89cb79d8df912d741c25ea7bce9061761 Mon Sep 17 00:00:00 2001 From: Mika Lindqvist Date: Fri, 6 Mar 2026 14:24:43 +0200 Subject: Relax alignment requirement in NEON_accum32. * UBSAN thinks only 16 byte alignment can be guaranteed. --- arch/arm/adler32_neon.c | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/arch/arm/adler32_neon.c b/arch/arm/adler32_neon.c index 5ba9b41178..9bbb293bd8 100644 --- a/arch/arm/adler32_neon.c +++ b/arch/arm/adler32_neon.c @@ -169,7 +169,7 @@ Z_FORCEINLINE static void NEON_accum32(uint32_t *s, const uint8_t *buf, size_t l int rem = len & 3; for (size_t i = 0; i < num_iter; ++i) { - uint8x16x4_t d0_d3 = vld1q_u8_x4_ex(buf, 256); + uint8x16x4_t d0_d3 = vld1q_u8_x4_ex(buf, 128); /* Unfortunately it doesn't look like there's a direct sum 8 bit to 32 * bit instruction, we'll have to make due summing to 16 bits first */ -- cgit 0.0.5-2-1-g0f52