diff mbox

[AArch64] Make argument of ld1 intrinsics const.

Message ID 1357556080-29402-1-git-send-email-james.greenhalgh@arm.com
State New
Headers show

Commit Message

James Greenhalgh Jan. 7, 2013, 10:54 a.m. UTC 
Hi,

This patch fixes the definitions of the vld1* intrinsics
to take a const-qualified argument.

I've tested this on aarch64-none-elf with no regressions.

Is this OK to commit?

Thanks,
James Greenhalgh

---
2013-01-07  James Greenhalgh  <james.greenhalgh@arm.com>

	* config/aarch64/arm_neon.h (vld1_dup_*): Make argument const.
	(vld1q_dup_*): Likewise.
	(vld1_*): Likewise.
	(vld1q_*): Likewise.
	(vld1_lane_*): Likewise.
	(vld1q_lane_*): Likewise.

Comments

Marcus Shawcroft Jan. 7, 2013, 2:55 p.m. UTC | #1 
On 07/01/13 10:54, James Greenhalgh wrote:
>
> Hi,
>
> This patch fixes the definitions of the vld1* intrinsics
> to take a const-qualified argument.
>
> I've tested this on aarch64-none-elf with no regressions.
>
> Is this OK to commit?
>
> Thanks,
> James Greenhalgh
>
> ---
> 2013-01-07  James Greenhalgh  <james.greenhalgh@arm.com>
>
> 	* config/aarch64/arm_neon.h (vld1_dup_*): Make argument const.
> 	(vld1q_dup_*): Likewise.
> 	(vld1_*): Likewise.
> 	(vld1q_*): Likewise.
> 	(vld1_lane_*): Likewise.
> 	(vld1q_lane_*): Likewise.
>

OK
diff mbox

Patch

diff --git a/gcc/config/aarch64/arm_neon.h b/gcc/config/aarch64/arm_neon.h
index e8fafa6..21fa428 100644
--- a/gcc/config/aarch64/arm_neon.h
+++ b/gcc/config/aarch64/arm_neon.h
@@ -8387,7 +8387,7 @@  vhsubq_u32 (uint32x4_t a, uint32x4_t b)
 }
 
 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
-vld1_dup_f32 (float32_t * a)
+vld1_dup_f32 (const float32_t * a)
 {
   float32x2_t result;
   __asm__ ("ld1r {%0.2s},[%1]"
@@ -8398,7 +8398,7 @@  vld1_dup_f32 (float32_t * a)
 }
 
 __extension__ static __inline float64x1_t __attribute__ ((__always_inline__))
-vld1_dup_f64 (float64_t * a)
+vld1_dup_f64 (const float64_t * a)
 {
   float64x1_t result;
   __asm__ ("ld1 {%0.1d},[%1]"
@@ -8409,7 +8409,7 @@  vld1_dup_f64 (float64_t * a)
 }
 
 __extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
-vld1_dup_p8 (poly8_t * a)
+vld1_dup_p8 (const poly8_t * a)
 {
   poly8x8_t result;
   __asm__ ("ld1r {%0.8b},[%1]"
@@ -8420,7 +8420,7 @@  vld1_dup_p8 (poly8_t * a)
 }
 
 __extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
-vld1_dup_p16 (poly16_t * a)
+vld1_dup_p16 (const poly16_t * a)
 {
   poly16x4_t result;
   __asm__ ("ld1r {%0.4h},[%1]"
@@ -8431,7 +8431,7 @@  vld1_dup_p16 (poly16_t * a)
 }
 
 __extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
-vld1_dup_s8 (int8_t * a)
+vld1_dup_s8 (const int8_t * a)
 {
   int8x8_t result;
   __asm__ ("ld1r {%0.8b},[%1]"
@@ -8442,7 +8442,7 @@  vld1_dup_s8 (int8_t * a)
 }
 
 __extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
-vld1_dup_s16 (int16_t * a)
+vld1_dup_s16 (const int16_t * a)
 {
   int16x4_t result;
   __asm__ ("ld1r {%0.4h},[%1]"
@@ -8453,7 +8453,7 @@  vld1_dup_s16 (int16_t * a)
 }
 
 __extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
-vld1_dup_s32 (int32_t * a)
+vld1_dup_s32 (const int32_t * a)
 {
   int32x2_t result;
   __asm__ ("ld1r {%0.2s},[%1]"
@@ -8464,7 +8464,7 @@  vld1_dup_s32 (int32_t * a)
 }
 
 __extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
-vld1_dup_s64 (int64_t * a)
+vld1_dup_s64 (const int64_t * a)
 {
   int64x1_t result;
   __asm__ ("ld1 {%0.1d},[%1]"
@@ -8475,7 +8475,7 @@  vld1_dup_s64 (int64_t * a)
 }
 
 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
-vld1_dup_u8 (uint8_t * a)
+vld1_dup_u8 (const uint8_t * a)
 {
   uint8x8_t result;
   __asm__ ("ld1r {%0.8b},[%1]"
@@ -8486,7 +8486,7 @@  vld1_dup_u8 (uint8_t * a)
 }
 
 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
-vld1_dup_u16 (uint16_t * a)
+vld1_dup_u16 (const uint16_t * a)
 {
   uint16x4_t result;
   __asm__ ("ld1r {%0.4h},[%1]"
@@ -8497,7 +8497,7 @@  vld1_dup_u16 (uint16_t * a)
 }
 
 __extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
-vld1_dup_u32 (uint32_t * a)
+vld1_dup_u32 (const uint32_t * a)
 {
   uint32x2_t result;
   __asm__ ("ld1r {%0.2s},[%1]"
@@ -8508,7 +8508,7 @@  vld1_dup_u32 (uint32_t * a)
 }
 
 __extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
-vld1_dup_u64 (uint64_t * a)
+vld1_dup_u64 (const uint64_t * a)
 {
   uint64x1_t result;
   __asm__ ("ld1 {%0.1d},[%1]"
@@ -8519,7 +8519,7 @@  vld1_dup_u64 (uint64_t * a)
 }
 
 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
-vld1_f32 (float32_t * a)
+vld1_f32 (const float32_t * a)
 {
   float32x2_t result;
   __asm__ ("ld1 {%0.2s},[%1]"
@@ -8530,7 +8530,7 @@  vld1_f32 (float32_t * a)
 }
 
 __extension__ static __inline float64x1_t __attribute__ ((__always_inline__))
-vld1_f64 (float64_t * a)
+vld1_f64 (const float64_t * a)
 {
   float64x1_t result;
   __asm__ ("ld1 {%0.1d},[%1]"
@@ -8544,7 +8544,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        float32x2_t b_ = (b);                                            \
-       float32_t * a_ = (a);                                            \
+       const float32_t * a_ = (a);                                      \
        float32x2_t result;                                              \
        __asm__ ("ld1 {%0.s}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8557,7 +8557,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        float64x1_t b_ = (b);                                            \
-       float64_t * a_ = (a);                                            \
+       const float64_t * a_ = (a);                                      \
        float64x1_t result;                                              \
        __asm__ ("ld1 {%0.d}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8570,7 +8570,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        poly8x8_t b_ = (b);                                              \
-       poly8_t * a_ = (a);                                              \
+       const poly8_t * a_ = (a);                                        \
        poly8x8_t result;                                                \
        __asm__ ("ld1 {%0.b}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8583,7 +8583,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        poly16x4_t b_ = (b);                                             \
-       poly16_t * a_ = (a);                                             \
+       const poly16_t * a_ = (a);                                       \
        poly16x4_t result;                                               \
        __asm__ ("ld1 {%0.h}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8596,7 +8596,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int8x8_t b_ = (b);                                               \
-       int8_t * a_ = (a);                                               \
+       const int8_t * a_ = (a);                                         \
        int8x8_t result;                                                 \
        __asm__ ("ld1 {%0.b}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8609,7 +8609,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int16x4_t b_ = (b);                                              \
-       int16_t * a_ = (a);                                              \
+       const int16_t * a_ = (a);                                        \
        int16x4_t result;                                                \
        __asm__ ("ld1 {%0.h}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8622,7 +8622,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int32x2_t b_ = (b);                                              \
-       int32_t * a_ = (a);                                              \
+       const int32_t * a_ = (a);                                        \
        int32x2_t result;                                                \
        __asm__ ("ld1 {%0.s}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8635,7 +8635,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int64x1_t b_ = (b);                                              \
-       int64_t * a_ = (a);                                              \
+       const int64_t * a_ = (a);                                        \
        int64x1_t result;                                                \
        __asm__ ("ld1 {%0.d}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8648,7 +8648,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint8x8_t b_ = (b);                                              \
-       uint8_t * a_ = (a);                                              \
+       const uint8_t * a_ = (a);                                        \
        uint8x8_t result;                                                \
        __asm__ ("ld1 {%0.b}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8661,7 +8661,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint16x4_t b_ = (b);                                             \
-       uint16_t * a_ = (a);                                             \
+       const uint16_t * a_ = (a);                                       \
        uint16x4_t result;                                               \
        __asm__ ("ld1 {%0.h}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8674,7 +8674,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint32x2_t b_ = (b);                                             \
-       uint32_t * a_ = (a);                                             \
+       const uint32_t * a_ = (a);                                       \
        uint32x2_t result;                                               \
        __asm__ ("ld1 {%0.s}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8687,7 +8687,7 @@  vld1_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint64x1_t b_ = (b);                                             \
-       uint64_t * a_ = (a);                                             \
+       const uint64_t * a_ = (a);                                       \
        uint64x1_t result;                                               \
        __asm__ ("ld1 {%0.d}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8697,7 +8697,7 @@  vld1_f64 (float64_t * a)
      })
 
 __extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
-vld1_p8 (poly8_t * a)
+vld1_p8 (const poly8_t * a)
 {
   poly8x8_t result;
   __asm__ ("ld1 {%0.8b}, [%1]"
@@ -8708,7 +8708,7 @@  vld1_p8 (poly8_t * a)
 }
 
 __extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
-vld1_p16 (poly16_t * a)
+vld1_p16 (const poly16_t * a)
 {
   poly16x4_t result;
   __asm__ ("ld1 {%0.4h}, [%1]"
@@ -8719,7 +8719,7 @@  vld1_p16 (poly16_t * a)
 }
 
 __extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
-vld1_s8 (int8_t * a)
+vld1_s8 (const int8_t * a)
 {
   int8x8_t result;
   __asm__ ("ld1 {%0.8b},[%1]"
@@ -8730,7 +8730,7 @@  vld1_s8 (int8_t * a)
 }
 
 __extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
-vld1_s16 (int16_t * a)
+vld1_s16 (const int16_t * a)
 {
   int16x4_t result;
   __asm__ ("ld1 {%0.4h},[%1]"
@@ -8741,7 +8741,7 @@  vld1_s16 (int16_t * a)
 }
 
 __extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
-vld1_s32 (int32_t * a)
+vld1_s32 (const int32_t * a)
 {
   int32x2_t result;
   __asm__ ("ld1 {%0.2s},[%1]"
@@ -8752,7 +8752,7 @@  vld1_s32 (int32_t * a)
 }
 
 __extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
-vld1_s64 (int64_t * a)
+vld1_s64 (const int64_t * a)
 {
   int64x1_t result;
   __asm__ ("ld1 {%0.1d},[%1]"
@@ -8763,7 +8763,7 @@  vld1_s64 (int64_t * a)
 }
 
 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
-vld1_u8 (uint8_t * a)
+vld1_u8 (const uint8_t * a)
 {
   uint8x8_t result;
   __asm__ ("ld1 {%0.8b},[%1]"
@@ -8774,7 +8774,7 @@  vld1_u8 (uint8_t * a)
 }
 
 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
-vld1_u16 (uint16_t * a)
+vld1_u16 (const uint16_t * a)
 {
   uint16x4_t result;
   __asm__ ("ld1 {%0.4h},[%1]"
@@ -8785,7 +8785,7 @@  vld1_u16 (uint16_t * a)
 }
 
 __extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
-vld1_u32 (uint32_t * a)
+vld1_u32 (const uint32_t * a)
 {
   uint32x2_t result;
   __asm__ ("ld1 {%0.2s},[%1]"
@@ -8796,7 +8796,7 @@  vld1_u32 (uint32_t * a)
 }
 
 __extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
-vld1_u64 (uint64_t * a)
+vld1_u64 (const uint64_t * a)
 {
   uint64x1_t result;
   __asm__ ("ld1 {%0.1d},[%1]"
@@ -8807,7 +8807,7 @@  vld1_u64 (uint64_t * a)
 }
 
 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
-vld1q_dup_f32 (float32_t * a)
+vld1q_dup_f32 (const float32_t * a)
 {
   float32x4_t result;
   __asm__ ("ld1r {%0.4s},[%1]"
@@ -8818,7 +8818,7 @@  vld1q_dup_f32 (float32_t * a)
 }
 
 __extension__ static __inline float64x2_t __attribute__ ((__always_inline__))
-vld1q_dup_f64 (float64_t * a)
+vld1q_dup_f64 (const float64_t * a)
 {
   float64x2_t result;
   __asm__ ("ld1r {%0.2d},[%1]"
@@ -8829,7 +8829,7 @@  vld1q_dup_f64 (float64_t * a)
 }
 
 __extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
-vld1q_dup_p8 (poly8_t * a)
+vld1q_dup_p8 (const poly8_t * a)
 {
   poly8x16_t result;
   __asm__ ("ld1r {%0.16b},[%1]"
@@ -8840,7 +8840,7 @@  vld1q_dup_p8 (poly8_t * a)
 }
 
 __extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
-vld1q_dup_p16 (poly16_t * a)
+vld1q_dup_p16 (const poly16_t * a)
 {
   poly16x8_t result;
   __asm__ ("ld1r {%0.8h},[%1]"
@@ -8851,7 +8851,7 @@  vld1q_dup_p16 (poly16_t * a)
 }
 
 __extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
-vld1q_dup_s8 (int8_t * a)
+vld1q_dup_s8 (const int8_t * a)
 {
   int8x16_t result;
   __asm__ ("ld1r {%0.16b},[%1]"
@@ -8862,7 +8862,7 @@  vld1q_dup_s8 (int8_t * a)
 }
 
 __extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
-vld1q_dup_s16 (int16_t * a)
+vld1q_dup_s16 (const int16_t * a)
 {
   int16x8_t result;
   __asm__ ("ld1r {%0.8h},[%1]"
@@ -8873,7 +8873,7 @@  vld1q_dup_s16 (int16_t * a)
 }
 
 __extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
-vld1q_dup_s32 (int32_t * a)
+vld1q_dup_s32 (const int32_t * a)
 {
   int32x4_t result;
   __asm__ ("ld1r {%0.4s},[%1]"
@@ -8884,7 +8884,7 @@  vld1q_dup_s32 (int32_t * a)
 }
 
 __extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
-vld1q_dup_s64 (int64_t * a)
+vld1q_dup_s64 (const int64_t * a)
 {
   int64x2_t result;
   __asm__ ("ld1r {%0.2d},[%1]"
@@ -8895,7 +8895,7 @@  vld1q_dup_s64 (int64_t * a)
 }
 
 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
-vld1q_dup_u8 (uint8_t * a)
+vld1q_dup_u8 (const uint8_t * a)
 {
   uint8x16_t result;
   __asm__ ("ld1r {%0.16b},[%1]"
@@ -8906,7 +8906,7 @@  vld1q_dup_u8 (uint8_t * a)
 }
 
 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
-vld1q_dup_u16 (uint16_t * a)
+vld1q_dup_u16 (const uint16_t * a)
 {
   uint16x8_t result;
   __asm__ ("ld1r {%0.8h},[%1]"
@@ -8917,7 +8917,7 @@  vld1q_dup_u16 (uint16_t * a)
 }
 
 __extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
-vld1q_dup_u32 (uint32_t * a)
+vld1q_dup_u32 (const uint32_t * a)
 {
   uint32x4_t result;
   __asm__ ("ld1r {%0.4s},[%1]"
@@ -8928,7 +8928,7 @@  vld1q_dup_u32 (uint32_t * a)
 }
 
 __extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
-vld1q_dup_u64 (uint64_t * a)
+vld1q_dup_u64 (const uint64_t * a)
 {
   uint64x2_t result;
   __asm__ ("ld1r {%0.2d},[%1]"
@@ -8939,7 +8939,7 @@  vld1q_dup_u64 (uint64_t * a)
 }
 
 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
-vld1q_f32 (float32_t * a)
+vld1q_f32 (const float32_t * a)
 {
   float32x4_t result;
   __asm__ ("ld1 {%0.4s},[%1]"
@@ -8950,7 +8950,7 @@  vld1q_f32 (float32_t * a)
 }
 
 __extension__ static __inline float64x2_t __attribute__ ((__always_inline__))
-vld1q_f64 (float64_t * a)
+vld1q_f64 (const float64_t * a)
 {
   float64x2_t result;
   __asm__ ("ld1 {%0.2d},[%1]"
@@ -8964,7 +8964,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        float32x4_t b_ = (b);                                            \
-       float32_t * a_ = (a);                                            \
+       const float32_t * a_ = (a);                                      \
        float32x4_t result;                                              \
        __asm__ ("ld1 {%0.s}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8977,7 +8977,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        float64x2_t b_ = (b);                                            \
-       float64_t * a_ = (a);                                            \
+       const float64_t * a_ = (a);                                      \
        float64x2_t result;                                              \
        __asm__ ("ld1 {%0.d}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -8990,7 +8990,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        poly8x16_t b_ = (b);                                             \
-       poly8_t * a_ = (a);                                              \
+       const poly8_t * a_ = (a);                                        \
        poly8x16_t result;                                               \
        __asm__ ("ld1 {%0.b}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9003,7 +9003,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        poly16x8_t b_ = (b);                                             \
-       poly16_t * a_ = (a);                                             \
+       const poly16_t * a_ = (a);                                       \
        poly16x8_t result;                                               \
        __asm__ ("ld1 {%0.h}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9016,7 +9016,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int8x16_t b_ = (b);                                              \
-       int8_t * a_ = (a);                                               \
+       const int8_t * a_ = (a);                                         \
        int8x16_t result;                                                \
        __asm__ ("ld1 {%0.b}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9029,7 +9029,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int16x8_t b_ = (b);                                              \
-       int16_t * a_ = (a);                                              \
+       const int16_t * a_ = (a);                                        \
        int16x8_t result;                                                \
        __asm__ ("ld1 {%0.h}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9042,7 +9042,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int32x4_t b_ = (b);                                              \
-       int32_t * a_ = (a);                                              \
+       const int32_t * a_ = (a);                                        \
        int32x4_t result;                                                \
        __asm__ ("ld1 {%0.s}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9055,7 +9055,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        int64x2_t b_ = (b);                                              \
-       int64_t * a_ = (a);                                              \
+       const int64_t * a_ = (a);                                        \
        int64x2_t result;                                                \
        __asm__ ("ld1 {%0.d}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9068,7 +9068,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint8x16_t b_ = (b);                                             \
-       uint8_t * a_ = (a);                                              \
+       const uint8_t * a_ = (a);                                        \
        uint8x16_t result;                                               \
        __asm__ ("ld1 {%0.b}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9081,7 +9081,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint16x8_t b_ = (b);                                             \
-       uint16_t * a_ = (a);                                             \
+       const uint16_t * a_ = (a);                                       \
        uint16x8_t result;                                               \
        __asm__ ("ld1 {%0.h}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9094,7 +9094,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint32x4_t b_ = (b);                                             \
-       uint32_t * a_ = (a);                                             \
+       const uint32_t * a_ = (a);                                       \
        uint32x4_t result;                                               \
        __asm__ ("ld1 {%0.s}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9107,7 +9107,7 @@  vld1q_f64 (float64_t * a)
   __extension__                                                         \
     ({                                                                  \
        uint64x2_t b_ = (b);                                             \
-       uint64_t * a_ = (a);                                             \
+       const uint64_t * a_ = (a);                                       \
        uint64x2_t result;                                               \
        __asm__ ("ld1 {%0.d}[%3],[%1]"                                   \
                 : "=w"(result)                                          \
@@ -9117,7 +9117,7 @@  vld1q_f64 (float64_t * a)
      })
 
 __extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
-vld1q_p8 (poly8_t * a)
+vld1q_p8 (const poly8_t * a)
 {
   poly8x16_t result;
   __asm__ ("ld1 {%0.16b},[%1]"
@@ -9128,7 +9128,7 @@  vld1q_p8 (poly8_t * a)
 }
 
 __extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
-vld1q_p16 (poly16_t * a)
+vld1q_p16 (const poly16_t * a)
 {
   poly16x8_t result;
   __asm__ ("ld1 {%0.8h},[%1]"
@@ -9139,7 +9139,7 @@  vld1q_p16 (poly16_t * a)
 }
 
 __extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
-vld1q_s8 (int8_t * a)
+vld1q_s8 (const int8_t * a)
 {
   int8x16_t result;
   __asm__ ("ld1 {%0.16b},[%1]"
@@ -9150,7 +9150,7 @@  vld1q_s8 (int8_t * a)
 }
 
 __extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
-vld1q_s16 (int16_t * a)
+vld1q_s16 (const int16_t * a)
 {
   int16x8_t result;
   __asm__ ("ld1 {%0.8h},[%1]"
@@ -9161,7 +9161,7 @@  vld1q_s16 (int16_t * a)
 }
 
 __extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
-vld1q_s32 (int32_t * a)
+vld1q_s32 (const int32_t * a)
 {
   int32x4_t result;
   __asm__ ("ld1 {%0.4s},[%1]"
@@ -9172,7 +9172,7 @@  vld1q_s32 (int32_t * a)
 }
 
 __extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
-vld1q_s64 (int64_t * a)
+vld1q_s64 (const int64_t * a)
 {
   int64x2_t result;
   __asm__ ("ld1 {%0.2d},[%1]"
@@ -9183,7 +9183,7 @@  vld1q_s64 (int64_t * a)
 }
 
 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
-vld1q_u8 (uint8_t * a)
+vld1q_u8 (const uint8_t * a)
 {
   uint8x16_t result;
   __asm__ ("ld1 {%0.16b},[%1]"
@@ -9194,7 +9194,7 @@  vld1q_u8 (uint8_t * a)
 }
 
 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
-vld1q_u16 (uint16_t * a)
+vld1q_u16 (const uint16_t * a)
 {
   uint16x8_t result;
   __asm__ ("ld1 {%0.8h},[%1]"
@@ -9205,7 +9205,7 @@  vld1q_u16 (uint16_t * a)
 }
 
 __extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
-vld1q_u32 (uint32_t * a)
+vld1q_u32 (const uint32_t * a)
 {
   uint32x4_t result;
   __asm__ ("ld1 {%0.4s},[%1]"
@@ -9216,7 +9216,7 @@  vld1q_u32 (uint32_t * a)
 }
 
 __extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
-vld1q_u64 (uint64_t * a)
+vld1q_u64 (const uint64_t * a)
 {
   uint64x2_t result;
   __asm__ ("ld1 {%0.2d},[%1]"