]> git.ipfire.org Git - thirdparty/gcc.git/commit
aarch64: arm_neon.h - Fix -Wincompatible-pointer-types errors
authorVictor Do Nascimento <victor.donascimento@arm.com>
Fri, 8 Dec 2023 16:37:31 +0000 (16:37 +0000)
committerVictor Do Nascimento <victor.donascimento@arm.com>
Mon, 11 Dec 2023 10:07:39 +0000 (10:07 +0000)
commit889341a897d3d2e9fb09de1a1c5e764a2c03424f
tree67fe5ea6e69369f611619a59d9584e28849a6066
parentf9b4dbb8ac75f96c4897ba9aafcaf0bbad4fbe44
aarch64: arm_neon.h - Fix -Wincompatible-pointer-types errors

In the Linux kernel, u64/s64 are [un]signed long long, not [un]signed
long.  This means that when the `arm_neon.h' header is used by the
kernel, any use of the `uint64_t' / `in64_t' types needs to be
correctly cast to the correct `__builtin_aarch64_simd_di' /
`__builtin_aarch64_simd_df' types when calling the relevant ACLE
builtins.

This patch adds the necessary fixes to ensure that `vstl1_*' and
`vldap1_*' intrinsics are correctly defined for use by the kernel.

gcc/ChangeLog:

* config/aarch64/arm_neon.h (vldap1_lane_u64): Add
`const' to `__builtin_aarch64_simd_di *' cast.
(vldap1q_lane_u64): Likewise.
(vldap1_lane_s64): Cast __src to `const __builtin_aarch64_simd_di *'.
(vldap1q_lane_s64): Likewise.
(vldap1_lane_f64): Cast __src to `const __builtin_aarch64_simd_df *'.
(vldap1q_lane_f64): Cast __src to `const __builtin_aarch64_simd_df *'.
(vldap1_lane_p64): Add `const' to `__builtin_aarch64_simd_di *' cast.
(vldap1q_lane_p64): Add `const' to `__builtin_aarch64_simd_di *' cast.
(vstl1_lane_u64): remove stray `const'.
(vstl1_lane_s64): Cast __src to `__builtin_aarch64_simd_di *'.
(vstl1q_lane_s64): Likewise.
(vstl1_lane_f64): Cast __src to `const __builtin_aarch64_simd_df *'.
(vstl1q_lane_f64): Likewise.
gcc/config/aarch64/arm_neon.h