diff options
| author | Victor Do Nascimento <victor.donascimento@arm.com> | 2023-12-08 16:37:31 +0000 |
|---|---|---|
| committer | Victor Do Nascimento <victor.donascimento@arm.com> | 2023-12-11 10:07:39 +0000 |
| commit | 889341a897d3d2e9fb09de1a1c5e764a2c03424f (patch) | |
| tree | 67fe5ea6e69369f611619a59d9584e28849a6066 /gcc/expr.cc | |
| parent | f9b4dbb8ac75f96c4897ba9aafcaf0bbad4fbe44 (diff) | |
| download | gcc-889341a897d3d2e9fb09de1a1c5e764a2c03424f.zip gcc-889341a897d3d2e9fb09de1a1c5e764a2c03424f.tar.gz gcc-889341a897d3d2e9fb09de1a1c5e764a2c03424f.tar.bz2 | |
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.
Diffstat (limited to 'gcc/expr.cc')
0 files changed, 0 insertions, 0 deletions