2014-05-23 Yvan Roux <yvan.roux@linaro.org>
+ Backport from trunk r209641, 209642.
+ 2014-04-22 Alex Velenko <Alex.Velenko@arm.com>
+
+ * config/aarch64/aarch64-builtins.c (TYPES_REINTERP): Removed.
+ (aarch64_types_signed_unsigned_qualifiers): Qualifier added.
+ (aarch64_types_signed_poly_qualifiers): Likewise.
+ (aarch64_types_unsigned_signed_qualifiers): Likewise.
+ (aarch64_types_poly_signed_qualifiers): Likewise.
+ (TYPES_REINTERP_SS): Type macro added.
+ (TYPES_REINTERP_SU): Likewise.
+ (TYPES_REINTERP_SP): Likewise.
+ (TYPES_REINTERP_US): Likewise.
+ (TYPES_REINTERP_PS): Likewise.
+ (aarch64_fold_builtin): New expression folding added.
+ * config/aarch64/aarch64-simd-builtins.def (REINTERP):
+ Declarations removed.
+ (REINTERP_SS): Declarations added.
+ (REINTERP_US): Likewise.
+ (REINTERP_PS): Likewise.
+ (REINTERP_SU): Likewise.
+ (REINTERP_SP): Likewise.
+ * config/aarch64/arm_neon.h (vreinterpret_p8_f64): Implemented.
+ (vreinterpretq_p8_f64): Likewise.
+ (vreinterpret_p16_f64): Likewise.
+ (vreinterpretq_p16_f64): Likewise.
+ (vreinterpret_f32_f64): Likewise.
+ (vreinterpretq_f32_f64): Likewise.
+ (vreinterpret_f64_f32): Likewise.
+ (vreinterpret_f64_p8): Likewise.
+ (vreinterpret_f64_p16): Likewise.
+ (vreinterpret_f64_s8): Likewise.
+ (vreinterpret_f64_s16): Likewise.
+ (vreinterpret_f64_s32): Likewise.
+ (vreinterpret_f64_s64): Likewise.
+ (vreinterpret_f64_u8): Likewise.
+ (vreinterpret_f64_u16): Likewise.
+ (vreinterpret_f64_u32): Likewise.
+ (vreinterpret_f64_u64): Likewise.
+ (vreinterpretq_f64_f32): Likewise.
+ (vreinterpretq_f64_p8): Likewise.
+ (vreinterpretq_f64_p16): Likewise.
+ (vreinterpretq_f64_s8): Likewise.
+ (vreinterpretq_f64_s16): Likewise.
+ (vreinterpretq_f64_s32): Likewise.
+ (vreinterpretq_f64_s64): Likewise.
+ (vreinterpretq_f64_u8): Likewise.
+ (vreinterpretq_f64_u16): Likewise.
+ (vreinterpretq_f64_u32): Likewise.
+ (vreinterpretq_f64_u64): Likewise.
+ (vreinterpret_s64_f64): Likewise.
+ (vreinterpretq_s64_f64): Likewise.
+ (vreinterpret_u64_f64): Likewise.
+ (vreinterpretq_u64_f64): Likewise.
+ (vreinterpret_s8_f64): Likewise.
+ (vreinterpretq_s8_f64): Likewise.
+ (vreinterpret_s16_f64): Likewise.
+ (vreinterpretq_s16_f64): Likewise.
+ (vreinterpret_s32_f64): Likewise.
+ (vreinterpretq_s32_f64): Likewise.
+ (vreinterpret_u8_f64): Likewise.
+ (vreinterpretq_u8_f64): Likewise.
+ (vreinterpret_u16_f64): Likewise.
+ (vreinterpretq_u16_f64): Likewise.
+ (vreinterpret_u32_f64): Likewise.
+ (vreinterpretq_u32_f64): Likewise.
+
+ 2014-04-22 Alex Velenko <Alex.Velenko@arm.com>
+
+ * config/aarch64/aarch64/aarch64-builtins.c (TYPES_REINTERP): Removed.
+ * config/aarch64/aarch64/aarch64-simd-builtins.def (REINTERP): Removed.
+ (vreinterpret_p8_s8): Likewise.
+ * config/aarch64/aarch64/arm_neon.h (vreinterpret_p8_s8): Uses cast.
+ (vreinterpret_p8_s16): Likewise.
+ (vreinterpret_p8_s32): Likewise.
+ (vreinterpret_p8_s64): Likewise.
+ (vreinterpret_p8_f32): Likewise.
+ (vreinterpret_p8_u8): Likewise.
+ (vreinterpret_p8_u16): Likewise.
+ (vreinterpret_p8_u32): Likewise.
+ (vreinterpret_p8_u64): Likewise.
+ (vreinterpret_p8_p16): Likewise.
+ (vreinterpretq_p8_s8): Likewise.
+ (vreinterpretq_p8_s16): Likewise.
+ (vreinterpretq_p8_s32): Likewise.
+ (vreinterpretq_p8_s64): Likewise.
+ (vreinterpretq_p8_f32): Likewise.
+ (vreinterpretq_p8_u8): Likewise.
+ (vreinterpretq_p8_u16): Likewise.
+ (vreinterpretq_p8_u32): Likewise.
+ (vreinterpretq_p8_u64): Likewise.
+ (vreinterpretq_p8_p16): Likewise.
+ (vreinterpret_p16_s8): Likewise.
+ (vreinterpret_p16_s16): Likewise.
+ (vreinterpret_p16_s32): Likewise.
+ (vreinterpret_p16_s64): Likewise.
+ (vreinterpret_p16_f32): Likewise.
+ (vreinterpret_p16_u8): Likewise.
+ (vreinterpret_p16_u16): Likewise.
+ (vreinterpret_p16_u32): Likewise.
+ (vreinterpret_p16_u64): Likewise.
+ (vreinterpret_p16_p8): Likewise.
+ (vreinterpretq_p16_s8): Likewise.
+ (vreinterpretq_p16_s16): Likewise.
+ (vreinterpretq_p16_s32): Likewise.
+ (vreinterpretq_p16_s64): Likewise.
+ (vreinterpretq_p16_f32): Likewise.
+ (vreinterpretq_p16_u8): Likewise.
+ (vreinterpretq_p16_u16): Likewise.
+ (vreinterpretq_p16_u32): Likewise.
+ (vreinterpretq_p16_u64): Likewise.
+ (vreinterpretq_p16_p8): Likewise.
+ (vreinterpret_f32_s8): Likewise.
+ (vreinterpret_f32_s16): Likewise.
+ (vreinterpret_f32_s32): Likewise.
+ (vreinterpret_f32_s64): Likewise.
+ (vreinterpret_f32_u8): Likewise.
+ (vreinterpret_f32_u16): Likewise.
+ (vreinterpret_f32_u32): Likewise.
+ (vreinterpret_f32_u64): Likewise.
+ (vreinterpret_f32_p8): Likewise.
+ (vreinterpret_f32_p16): Likewise.
+ (vreinterpretq_f32_s8): Likewise.
+ (vreinterpretq_f32_s16): Likewise.
+ (vreinterpretq_f32_s32): Likewise.
+ (vreinterpretq_f32_s64): Likewise.
+ (vreinterpretq_f32_u8): Likewise.
+ (vreinterpretq_f32_u16): Likewise.
+ (vreinterpretq_f32_u32): Likewise.
+ (vreinterpretq_f32_u64): Likewise.
+ (vreinterpretq_f32_p8): Likewise.
+ (vreinterpretq_f32_p16): Likewise.
+ (vreinterpret_s64_s8): Likewise.
+ (vreinterpret_s64_s16): Likewise.
+ (vreinterpret_s64_s32): Likewise.
+ (vreinterpret_s64_f32): Likewise.
+ (vreinterpret_s64_u8): Likewise.
+ (vreinterpret_s64_u16): Likewise.
+ (vreinterpret_s64_u32): Likewise.
+ (vreinterpret_s64_u64): Likewise.
+ (vreinterpret_s64_p8): Likewise.
+ (vreinterpret_s64_p16): Likewise.
+ (vreinterpretq_s64_s8): Likewise.
+ (vreinterpretq_s64_s16): Likewise.
+ (vreinterpretq_s64_s32): Likewise.
+ (vreinterpretq_s64_f32): Likewise.
+ (vreinterpretq_s64_u8): Likewise.
+ (vreinterpretq_s64_u16): Likewise.
+ (vreinterpretq_s64_u32): Likewise.
+ (vreinterpretq_s64_u64): Likewise.
+ (vreinterpretq_s64_p8): Likewise.
+ (vreinterpretq_s64_p16): Likewise.
+ (vreinterpret_u64_s8): Likewise.
+ (vreinterpret_u64_s16): Likewise.
+ (vreinterpret_u64_s32): Likewise.
+ (vreinterpret_u64_s64): Likewise.
+ (vreinterpret_u64_f32): Likewise.
+ (vreinterpret_u64_u8): Likewise.
+ (vreinterpret_u64_u16): Likewise.
+ (vreinterpret_u64_u32): Likewise.
+ (vreinterpret_u64_p8): Likewise.
+ (vreinterpret_u64_p16): Likewise.
+ (vreinterpretq_u64_s8): Likewise.
+ (vreinterpretq_u64_s16): Likewise.
+ (vreinterpretq_u64_s32): Likewise.
+ (vreinterpretq_u64_s64): Likewise.
+ (vreinterpretq_u64_f32): Likewise.
+ (vreinterpretq_u64_u8): Likewise.
+ (vreinterpretq_u64_u16): Likewise.
+ (vreinterpretq_u64_u32): Likewise.
+ (vreinterpretq_u64_p8): Likewise.
+ (vreinterpretq_u64_p16): Likewise.
+ (vreinterpret_s8_s16): Likewise.
+ (vreinterpret_s8_s32): Likewise.
+ (vreinterpret_s8_s64): Likewise.
+ (vreinterpret_s8_f32): Likewise.
+ (vreinterpret_s8_u8): Likewise.
+ (vreinterpret_s8_u16): Likewise.
+ (vreinterpret_s8_u32): Likewise.
+ (vreinterpret_s8_u64): Likewise.
+ (vreinterpret_s8_p8): Likewise.
+ (vreinterpret_s8_p16): Likewise.
+ (vreinterpretq_s8_s16): Likewise.
+ (vreinterpretq_s8_s32): Likewise.
+ (vreinterpretq_s8_s64): Likewise.
+ (vreinterpretq_s8_f32): Likewise.
+ (vreinterpretq_s8_u8): Likewise.
+ (vreinterpretq_s8_u16): Likewise.
+ (vreinterpretq_s8_u32): Likewise.
+ (vreinterpretq_s8_u64): Likewise.
+ (vreinterpretq_s8_p8): Likewise.
+ (vreinterpretq_s8_p16): Likewise.
+ (vreinterpret_s16_s8): Likewise.
+ (vreinterpret_s16_s32): Likewise.
+ (vreinterpret_s16_s64): Likewise.
+ (vreinterpret_s16_f32): Likewise.
+ (vreinterpret_s16_u8): Likewise.
+ (vreinterpret_s16_u16): Likewise.
+ (vreinterpret_s16_u32): Likewise.
+ (vreinterpret_s16_u64): Likewise.
+ (vreinterpret_s16_p8): Likewise.
+ (vreinterpret_s16_p16): Likewise.
+ (vreinterpretq_s16_s8): Likewise.
+ (vreinterpretq_s16_s32): Likewise.
+ (vreinterpretq_s16_s64): Likewise.
+ (vreinterpretq_s16_f32): Likewise.
+ (vreinterpretq_s16_u8): Likewise.
+ (vreinterpretq_s16_u16): Likewise.
+ (vreinterpretq_s16_u32): Likewise.
+ (vreinterpretq_s16_u64): Likewise.
+ (vreinterpretq_s16_p8): Likewise.
+ (vreinterpretq_s16_p16): Likewise.
+ (vreinterpret_s32_s8): Likewise.
+ (vreinterpret_s32_s16): Likewise.
+ (vreinterpret_s32_s64): Likewise.
+ (vreinterpret_s32_f32): Likewise.
+ (vreinterpret_s32_u8): Likewise.
+ (vreinterpret_s32_u16): Likewise.
+ (vreinterpret_s32_u32): Likewise.
+ (vreinterpret_s32_u64): Likewise.
+ (vreinterpret_s32_p8): Likewise.
+ (vreinterpret_s32_p16): Likewise.
+ (vreinterpretq_s32_s8): Likewise.
+ (vreinterpretq_s32_s16): Likewise.
+ (vreinterpretq_s32_s64): Likewise.
+ (vreinterpretq_s32_f32): Likewise.
+ (vreinterpretq_s32_u8): Likewise.
+ (vreinterpretq_s32_u16): Likewise.
+ (vreinterpretq_s32_u32): Likewise.
+ (vreinterpretq_s32_u64): Likewise.
+ (vreinterpretq_s32_p8): Likewise.
+ (vreinterpretq_s32_p16): Likewise.
+ (vreinterpret_u8_s8): Likewise.
+ (vreinterpret_u8_s16): Likewise.
+ (vreinterpret_u8_s32): Likewise.
+ (vreinterpret_u8_s64): Likewise.
+ (vreinterpret_u8_f32): Likewise.
+ (vreinterpret_u8_u16): Likewise.
+ (vreinterpret_u8_u32): Likewise.
+ (vreinterpret_u8_u64): Likewise.
+ (vreinterpret_u8_p8): Likewise.
+ (vreinterpret_u8_p16): Likewise.
+ (vreinterpretq_u8_s8): Likewise.
+ (vreinterpretq_u8_s16): Likewise.
+ (vreinterpretq_u8_s32): Likewise.
+ (vreinterpretq_u8_s64): Likewise.
+ (vreinterpretq_u8_f32): Likewise.
+ (vreinterpretq_u8_u16): Likewise.
+ (vreinterpretq_u8_u32): Likewise.
+ (vreinterpretq_u8_u64): Likewise.
+ (vreinterpretq_u8_p8): Likewise.
+ (vreinterpretq_u8_p16): Likewise.
+ (vreinterpret_u16_s8): Likewise.
+ (vreinterpret_u16_s16): Likewise.
+ (vreinterpret_u16_s32): Likewise.
+ (vreinterpret_u16_s64): Likewise.
+ (vreinterpret_u16_f32): Likewise.
+ (vreinterpret_u16_u8): Likewise.
+ (vreinterpret_u16_u32): Likewise.
+ (vreinterpret_u16_u64): Likewise.
+ (vreinterpret_u16_p8): Likewise.
+ (vreinterpret_u16_p16): Likewise.
+ (vreinterpretq_u16_s8): Likewise.
+ (vreinterpretq_u16_s16): Likewise.
+ (vreinterpretq_u16_s32): Likewise.
+ (vreinterpretq_u16_s64): Likewise.
+ (vreinterpretq_u16_f32): Likewise.
+ (vreinterpretq_u16_u8): Likewise.
+ (vreinterpretq_u16_u32): Likewise.
+ (vreinterpretq_u16_u64): Likewise.
+ (vreinterpretq_u16_p8): Likewise.
+ (vreinterpretq_u16_p16): Likewise.
+ (vreinterpret_u32_s8): Likewise.
+ (vreinterpret_u32_s16): Likewise.
+ (vreinterpret_u32_s32): Likewise.
+ (vreinterpret_u32_s64): Likewise.
+ (vreinterpret_u32_f32): Likewise.
+ (vreinterpret_u32_u8): Likewise.
+ (vreinterpret_u32_u16): Likewise.
+ (vreinterpret_u32_u64): Likewise.
+ (vreinterpret_u32_p8): Likewise.
+ (vreinterpret_u32_p16): Likewise.
+ (vreinterpretq_u32_s8): Likewise.
+ (vreinterpretq_u32_s16): Likewise.
+ (vreinterpretq_u32_s32): Likewise.
+ (vreinterpretq_u32_s64): Likewise.
+ (vreinterpretq_u32_f32): Likewise.
+ (vreinterpretq_u32_u8): Likewise.
+ (vreinterpretq_u32_u16): Likewise.
+ (vreinterpretq_u32_u64): Likewise.
+ (vreinterpretq_u32_p8): Likewise.
+ (vreinterpretq_u32_p16): Likewise.
+
+2014-05-23 Yvan Roux <yvan.roux@linaro.org>
+
Backport from trunk r209640.
2014-04-22 Alex Velenko <Alex.Velenko@arm.com>
/* vreinterpret */
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
+vreinterpret_p8_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv8qidf_ps (__a);
+}
+
+__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_s8 (int8x8_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv8qi (__a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_s16 (int16x4_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv4hi (__a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_s32 (int32x2_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv2si (__a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_s64 (int64x1_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qidi (__a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_f32 (float32x2_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv2sf (__a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_u8 (uint8x8_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv8qi ((int8x8_t) __a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_u16 (uint16x4_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv4hi ((int16x4_t) __a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_u32 (uint32x2_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv2si ((int32x2_t) __a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_u64 (uint64x1_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qidi ((int64x1_t) __a);
+ return (poly8x8_t) __a;
}
__extension__ static __inline poly8x8_t __attribute__ ((__always_inline__))
vreinterpret_p8_p16 (poly16x4_t __a)
{
- return (poly8x8_t) __builtin_aarch64_reinterpretv8qiv4hi ((int16x4_t) __a);
+ return (poly8x8_t) __a;
+}
+
+__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
+vreinterpretq_p8_f64 (float64x2_t __a)
+{
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_s8 (int8x16_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv16qi (__a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_s16 (int16x8_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv8hi (__a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_s32 (int32x4_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv4si (__a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_s64 (int64x2_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv2di (__a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_f32 (float32x4_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv4sf (__a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_u8 (uint8x16_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv16qi ((int8x16_t)
- __a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_u16 (uint16x8_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv8hi ((int16x8_t)
- __a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_u32 (uint32x4_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv4si ((int32x4_t)
- __a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_u64 (uint64x2_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv2di ((int64x2_t)
- __a);
+ return (poly8x16_t) __a;
}
__extension__ static __inline poly8x16_t __attribute__ ((__always_inline__))
vreinterpretq_p8_p16 (poly16x8_t __a)
{
- return (poly8x16_t) __builtin_aarch64_reinterpretv16qiv8hi ((int16x8_t)
- __a);
+ return (poly8x16_t) __a;
+}
+
+__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
+vreinterpret_p16_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv4hidf_ps (__a);
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_s8 (int8x8_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv8qi (__a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_s16 (int16x4_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv4hi (__a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_s32 (int32x2_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv2si (__a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_s64 (int64x1_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hidi (__a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_f32 (float32x2_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv2sf (__a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_u8 (uint8x8_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv8qi ((int8x8_t) __a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_u16 (uint16x4_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv4hi ((int16x4_t) __a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_u32 (uint32x2_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv2si ((int32x2_t) __a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_u64 (uint64x1_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hidi ((int64x1_t) __a);
+ return (poly16x4_t) __a;
}
__extension__ static __inline poly16x4_t __attribute__ ((__always_inline__))
vreinterpret_p16_p8 (poly8x8_t __a)
{
- return (poly16x4_t) __builtin_aarch64_reinterpretv4hiv8qi ((int8x8_t) __a);
+ return (poly16x4_t) __a;
+}
+
+__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
+vreinterpretq_p16_f64 (float64x2_t __a)
+{
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_s8 (int8x16_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv16qi (__a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_s16 (int16x8_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv8hi (__a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_s32 (int32x4_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv4si (__a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_s64 (int64x2_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv2di (__a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_f32 (float32x4_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv4sf (__a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_u8 (uint8x16_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv16qi ((int8x16_t)
- __a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_u16 (uint16x8_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv8hi ((int16x8_t) __a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_u32 (uint32x4_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv4si ((int32x4_t) __a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_u64 (uint64x2_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv2di ((int64x2_t) __a);
+ return (poly16x8_t) __a;
}
__extension__ static __inline poly16x8_t __attribute__ ((__always_inline__))
vreinterpretq_p16_p8 (poly8x16_t __a)
{
- return (poly16x8_t) __builtin_aarch64_reinterpretv8hiv16qi ((int8x16_t)
- __a);
+ return (poly16x8_t) __a;
+}
+
+__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
+vreinterpret_f32_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv2sfdf (__a);
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_s8 (int8x8_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv8qi (__a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_s16 (int16x4_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv4hi (__a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_s32 (int32x2_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv2si (__a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_s64 (int64x1_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfdi (__a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_u8 (uint8x8_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv8qi ((int8x8_t) __a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_u16 (uint16x4_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv4hi ((int16x4_t)
- __a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_u32 (uint32x2_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv2si ((int32x2_t)
- __a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_u64 (uint64x1_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfdi ((int64x1_t) __a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_p8 (poly8x8_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv8qi ((int8x8_t) __a);
+ return (float32x2_t) __a;
}
__extension__ static __inline float32x2_t __attribute__ ((__always_inline__))
vreinterpret_f32_p16 (poly16x4_t __a)
{
- return (float32x2_t) __builtin_aarch64_reinterpretv2sfv4hi ((int16x4_t)
- __a);
+ return (float32x2_t) __a;
+}
+
+__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
+vreinterpretq_f32_f64 (float64x2_t __a)
+{
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_s8 (int8x16_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv16qi (__a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_s16 (int16x8_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv8hi (__a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_s32 (int32x4_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv4si (__a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_s64 (int64x2_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv2di (__a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_u8 (uint8x16_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv16qi ((int8x16_t)
- __a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_u16 (uint16x8_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv8hi ((int16x8_t)
- __a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_u32 (uint32x4_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv4si ((int32x4_t)
- __a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_u64 (uint64x2_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv2di ((int64x2_t)
- __a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_p8 (poly8x16_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv16qi ((int8x16_t)
- __a);
+ return (float32x4_t) __a;
}
__extension__ static __inline float32x4_t __attribute__ ((__always_inline__))
vreinterpretq_f32_p16 (poly16x8_t __a)
{
- return (float32x4_t) __builtin_aarch64_reinterpretv4sfv8hi ((int16x8_t)
- __a);
+ return (float32x4_t) __a;
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_f32 (float32x2_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv2sf (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_p8 (poly8x8_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv8qi_sp (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_p16 (poly16x4_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv4hi_sp (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_s8 (int8x8_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv8qi (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_s16 (int16x4_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv4hi (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_s32 (int32x2_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv2si (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_s64 (int64x1_t __a)
+{
+ return __builtin_aarch64_createdf ((uint64_t) vget_lane_s64 (__a, 0));
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_u8 (uint8x8_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv8qi_su (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_u16 (uint16x4_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv4hi_su (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_u32 (uint32x2_t __a)
+{
+ return __builtin_aarch64_reinterpretdfv2si_su (__a);
+}
+
+__extension__ static __inline float64x1_t __attribute__((__always_inline__))
+vreinterpret_f64_u64 (uint64x1_t __a)
+{
+ return __builtin_aarch64_createdf (vget_lane_u64 (__a, 0));
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_f32 (float32x4_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_p8 (poly8x16_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_p16 (poly16x8_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_s8 (int8x16_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_s16 (int16x8_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_s32 (int32x4_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_s64 (int64x2_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_u8 (uint8x16_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_u16 (uint16x8_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_u32 (uint32x4_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline float64x2_t __attribute__((__always_inline__))
+vreinterpretq_f64_u64 (uint64x2_t __a)
+{
+ return (float64x2_t) __a;
+}
+
+__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
+vreinterpret_s64_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretdidf (__a);
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_s8 (int8x8_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv8qi (__a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_s16 (int16x4_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv4hi (__a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_s32 (int32x2_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv2si (__a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_f32 (float32x2_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv2sf (__a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_u8 (uint8x8_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv8qi ((int8x8_t) __a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_u16 (uint16x4_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv4hi ((int16x4_t) __a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_u32 (uint32x2_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv2si ((int32x2_t) __a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_u64 (uint64x1_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdidi ((int64x1_t) __a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_p8 (poly8x8_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv8qi ((int8x8_t) __a);
+ return (int64x1_t) __a;
}
__extension__ static __inline int64x1_t __attribute__ ((__always_inline__))
vreinterpret_s64_p16 (poly16x4_t __a)
{
- return (int64x1_t) __builtin_aarch64_reinterpretdiv4hi ((int16x4_t) __a);
+ return (int64x1_t) __a;
+}
+
+__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
+vreinterpretq_s64_f64 (float64x2_t __a)
+{
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_s8 (int8x16_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div16qi (__a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_s16 (int16x8_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div8hi (__a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_s32 (int32x4_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div4si (__a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_f32 (float32x4_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div4sf (__a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_u8 (uint8x16_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div16qi ((int8x16_t) __a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_u16 (uint16x8_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div8hi ((int16x8_t) __a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_u32 (uint32x4_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div4si ((int32x4_t) __a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_u64 (uint64x2_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div2di ((int64x2_t) __a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_p8 (poly8x16_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div16qi ((int8x16_t) __a);
+ return (int64x2_t) __a;
}
__extension__ static __inline int64x2_t __attribute__ ((__always_inline__))
vreinterpretq_s64_p16 (poly16x8_t __a)
{
- return (int64x2_t) __builtin_aarch64_reinterpretv2div8hi ((int16x8_t) __a);
+ return (int64x2_t) __a;
+}
+
+__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
+vreinterpret_u64_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretdidf_us (__a);
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_s8 (int8x8_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv8qi (__a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_s16 (int16x4_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv4hi (__a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_s32 (int32x2_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv2si (__a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_s64 (int64x1_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdidi (__a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_f32 (float32x2_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv2sf (__a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_u8 (uint8x8_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv8qi ((int8x8_t) __a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_u16 (uint16x4_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv4hi ((int16x4_t) __a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_u32 (uint32x2_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv2si ((int32x2_t) __a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_p8 (poly8x8_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv8qi ((int8x8_t) __a);
+ return (uint64x1_t) __a;
}
__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
vreinterpret_u64_p16 (poly16x4_t __a)
{
- return (uint64x1_t) __builtin_aarch64_reinterpretdiv4hi ((int16x4_t) __a);
+ return (uint64x1_t) __a;
+}
+
+__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
+vreinterpretq_u64_f64 (float64x2_t __a)
+{
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_s8 (int8x16_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div16qi (__a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_s16 (int16x8_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div8hi (__a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_s32 (int32x4_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div4si (__a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_s64 (int64x2_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div2di (__a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_f32 (float32x4_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div4sf (__a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_u8 (uint8x16_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div16qi ((int8x16_t)
- __a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_u16 (uint16x8_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div8hi ((int16x8_t) __a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_u32 (uint32x4_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div4si ((int32x4_t) __a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_p8 (poly8x16_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div16qi ((int8x16_t)
- __a);
+ return (uint64x2_t) __a;
}
__extension__ static __inline uint64x2_t __attribute__ ((__always_inline__))
vreinterpretq_u64_p16 (poly16x8_t __a)
{
- return (uint64x2_t) __builtin_aarch64_reinterpretv2div8hi ((int16x8_t) __a);
+ return (uint64x2_t) __a;
+}
+
+__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
+vreinterpret_s8_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv8qidf (__a);
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_s16 (int16x4_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv4hi (__a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_s32 (int32x2_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv2si (__a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_s64 (int64x1_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qidi (__a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_f32 (float32x2_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv2sf (__a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_u8 (uint8x8_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv8qi ((int8x8_t) __a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_u16 (uint16x4_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv4hi ((int16x4_t) __a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_u32 (uint32x2_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv2si ((int32x2_t) __a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_u64 (uint64x1_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qidi ((int64x1_t) __a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_p8 (poly8x8_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv8qi ((int8x8_t) __a);
+ return (int8x8_t) __a;
}
__extension__ static __inline int8x8_t __attribute__ ((__always_inline__))
vreinterpret_s8_p16 (poly16x4_t __a)
{
- return (int8x8_t) __builtin_aarch64_reinterpretv8qiv4hi ((int16x4_t) __a);
+ return (int8x8_t) __a;
+}
+
+__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
+vreinterpretq_s8_f64 (float64x2_t __a)
+{
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_s16 (int16x8_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv8hi (__a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_s32 (int32x4_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv4si (__a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_s64 (int64x2_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv2di (__a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_f32 (float32x4_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv4sf (__a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_u8 (uint8x16_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv16qi ((int8x16_t)
- __a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_u16 (uint16x8_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv8hi ((int16x8_t) __a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_u32 (uint32x4_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv4si ((int32x4_t) __a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_u64 (uint64x2_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv2di ((int64x2_t) __a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_p8 (poly8x16_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv16qi ((int8x16_t)
- __a);
+ return (int8x16_t) __a;
}
__extension__ static __inline int8x16_t __attribute__ ((__always_inline__))
vreinterpretq_s8_p16 (poly16x8_t __a)
{
- return (int8x16_t) __builtin_aarch64_reinterpretv16qiv8hi ((int16x8_t) __a);
+ return (int8x16_t) __a;
+}
+
+__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
+vreinterpret_s16_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv4hidf (__a);
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_s8 (int8x8_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv8qi (__a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_s32 (int32x2_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv2si (__a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_s64 (int64x1_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hidi (__a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_f32 (float32x2_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv2sf (__a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_u8 (uint8x8_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv8qi ((int8x8_t) __a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_u16 (uint16x4_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv4hi ((int16x4_t) __a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_u32 (uint32x2_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv2si ((int32x2_t) __a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_u64 (uint64x1_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hidi ((int64x1_t) __a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_p8 (poly8x8_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv8qi ((int8x8_t) __a);
+ return (int16x4_t) __a;
}
__extension__ static __inline int16x4_t __attribute__ ((__always_inline__))
vreinterpret_s16_p16 (poly16x4_t __a)
{
- return (int16x4_t) __builtin_aarch64_reinterpretv4hiv4hi ((int16x4_t) __a);
+ return (int16x4_t) __a;
+}
+
+__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
+vreinterpretq_s16_f64 (float64x2_t __a)
+{
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_s8 (int8x16_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv16qi (__a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_s32 (int32x4_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv4si (__a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_s64 (int64x2_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv2di (__a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_f32 (float32x4_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv4sf (__a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_u8 (uint8x16_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv16qi ((int8x16_t) __a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_u16 (uint16x8_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv8hi ((int16x8_t) __a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_u32 (uint32x4_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv4si ((int32x4_t) __a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_u64 (uint64x2_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv2di ((int64x2_t) __a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_p8 (poly8x16_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv16qi ((int8x16_t) __a);
+ return (int16x8_t) __a;
}
__extension__ static __inline int16x8_t __attribute__ ((__always_inline__))
vreinterpretq_s16_p16 (poly16x8_t __a)
{
- return (int16x8_t) __builtin_aarch64_reinterpretv8hiv8hi ((int16x8_t) __a);
+ return (int16x8_t) __a;
+}
+
+__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
+vreinterpret_s32_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv2sidf (__a);
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_s8 (int8x8_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv8qi (__a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_s16 (int16x4_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv4hi (__a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_s64 (int64x1_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2sidi (__a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_f32 (float32x2_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv2sf (__a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_u8 (uint8x8_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv8qi ((int8x8_t) __a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_u16 (uint16x4_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv4hi ((int16x4_t) __a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_u32 (uint32x2_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv2si ((int32x2_t) __a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_u64 (uint64x1_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2sidi ((int64x1_t) __a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_p8 (poly8x8_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv8qi ((int8x8_t) __a);
+ return (int32x2_t) __a;
}
__extension__ static __inline int32x2_t __attribute__ ((__always_inline__))
vreinterpret_s32_p16 (poly16x4_t __a)
{
- return (int32x2_t) __builtin_aarch64_reinterpretv2siv4hi ((int16x4_t) __a);
+ return (int32x2_t) __a;
+}
+
+__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
+vreinterpretq_s32_f64 (float64x2_t __a)
+{
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_s8 (int8x16_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv16qi (__a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_s16 (int16x8_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv8hi (__a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_s64 (int64x2_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv2di (__a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_f32 (float32x4_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv4sf (__a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_u8 (uint8x16_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv16qi ((int8x16_t) __a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_u16 (uint16x8_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv8hi ((int16x8_t) __a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_u32 (uint32x4_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv4si ((int32x4_t) __a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_u64 (uint64x2_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv2di ((int64x2_t) __a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_p8 (poly8x16_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv16qi ((int8x16_t) __a);
+ return (int32x4_t) __a;
}
__extension__ static __inline int32x4_t __attribute__ ((__always_inline__))
vreinterpretq_s32_p16 (poly16x8_t __a)
{
- return (int32x4_t) __builtin_aarch64_reinterpretv4siv8hi ((int16x8_t) __a);
+ return (int32x4_t) __a;
+}
+
+__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
+vreinterpret_u8_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv8qidf_us (__a);
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_s8 (int8x8_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv8qi (__a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_s16 (int16x4_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv4hi (__a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_s32 (int32x2_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv2si (__a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_s64 (int64x1_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qidi (__a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_f32 (float32x2_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv2sf (__a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_u16 (uint16x4_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv4hi ((int16x4_t) __a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_u32 (uint32x2_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv2si ((int32x2_t) __a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_u64 (uint64x1_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qidi ((int64x1_t) __a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_p8 (poly8x8_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv8qi ((int8x8_t) __a);
+ return (uint8x8_t) __a;
}
__extension__ static __inline uint8x8_t __attribute__ ((__always_inline__))
vreinterpret_u8_p16 (poly16x4_t __a)
{
- return (uint8x8_t) __builtin_aarch64_reinterpretv8qiv4hi ((int16x4_t) __a);
+ return (uint8x8_t) __a;
+}
+
+__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
+vreinterpretq_u8_f64 (float64x2_t __a)
+{
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_s8 (int8x16_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv16qi (__a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_s16 (int16x8_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv8hi (__a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_s32 (int32x4_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv4si (__a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_s64 (int64x2_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv2di (__a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_f32 (float32x4_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv4sf (__a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_u16 (uint16x8_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv8hi ((int16x8_t)
- __a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_u32 (uint32x4_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv4si ((int32x4_t)
- __a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_u64 (uint64x2_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv2di ((int64x2_t)
- __a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_p8 (poly8x16_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv16qi ((int8x16_t)
- __a);
+ return (uint8x16_t) __a;
}
__extension__ static __inline uint8x16_t __attribute__ ((__always_inline__))
vreinterpretq_u8_p16 (poly16x8_t __a)
{
- return (uint8x16_t) __builtin_aarch64_reinterpretv16qiv8hi ((int16x8_t)
- __a);
+ return (uint8x16_t) __a;
+}
+
+__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
+vreinterpret_u16_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv4hidf_us (__a);
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_s8 (int8x8_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv8qi (__a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_s16 (int16x4_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv4hi (__a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_s32 (int32x2_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv2si (__a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_s64 (int64x1_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hidi (__a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_f32 (float32x2_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv2sf (__a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_u8 (uint8x8_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv8qi ((int8x8_t) __a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_u32 (uint32x2_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv2si ((int32x2_t) __a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_u64 (uint64x1_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hidi ((int64x1_t) __a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_p8 (poly8x8_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv8qi ((int8x8_t) __a);
+ return (uint16x4_t) __a;
}
__extension__ static __inline uint16x4_t __attribute__ ((__always_inline__))
vreinterpret_u16_p16 (poly16x4_t __a)
{
- return (uint16x4_t) __builtin_aarch64_reinterpretv4hiv4hi ((int16x4_t) __a);
+ return (uint16x4_t) __a;
+}
+
+__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
+vreinterpretq_u16_f64 (float64x2_t __a)
+{
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_s8 (int8x16_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv16qi (__a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_s16 (int16x8_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv8hi (__a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_s32 (int32x4_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv4si (__a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_s64 (int64x2_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv2di (__a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_f32 (float32x4_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv4sf (__a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_u8 (uint8x16_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv16qi ((int8x16_t)
- __a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_u32 (uint32x4_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv4si ((int32x4_t) __a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_u64 (uint64x2_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv2di ((int64x2_t) __a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_p8 (poly8x16_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv16qi ((int8x16_t)
- __a);
+ return (uint16x8_t) __a;
}
__extension__ static __inline uint16x8_t __attribute__ ((__always_inline__))
vreinterpretq_u16_p16 (poly16x8_t __a)
{
- return (uint16x8_t) __builtin_aarch64_reinterpretv8hiv8hi ((int16x8_t) __a);
+ return (uint16x8_t) __a;
+}
+
+__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
+vreinterpret_u32_f64 (float64x1_t __a)
+{
+ return __builtin_aarch64_reinterpretv2sidf_us (__a);
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_s8 (int8x8_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv8qi (__a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_s16 (int16x4_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv4hi (__a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_s32 (int32x2_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv2si (__a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_s64 (int64x1_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2sidi (__a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_f32 (float32x2_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv2sf (__a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_u8 (uint8x8_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv8qi ((int8x8_t) __a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_u16 (uint16x4_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv4hi ((int16x4_t) __a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_u64 (uint64x1_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2sidi ((int64x1_t) __a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_p8 (poly8x8_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv8qi ((int8x8_t) __a);
+ return (uint32x2_t) __a;
}
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
vreinterpret_u32_p16 (poly16x4_t __a)
{
- return (uint32x2_t) __builtin_aarch64_reinterpretv2siv4hi ((int16x4_t) __a);
+ return (uint32x2_t) __a;
+}
+
+__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
+vreinterpretq_u32_f64 (float64x2_t __a)
+{
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_s8 (int8x16_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv16qi (__a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_s16 (int16x8_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv8hi (__a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_s32 (int32x4_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv4si (__a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_s64 (int64x2_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv2di (__a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_f32 (float32x4_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv4sf (__a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_u8 (uint8x16_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv16qi ((int8x16_t)
- __a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_u16 (uint16x8_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv8hi ((int16x8_t) __a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_u64 (uint64x2_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv2di ((int64x2_t) __a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_p8 (poly8x16_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv16qi ((int8x16_t)
- __a);
+ return (uint32x4_t) __a;
}
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vreinterpretq_u32_p16 (poly16x8_t __a)
{
- return (uint32x4_t) __builtin_aarch64_reinterpretv4siv8hi ((int16x8_t) __a);
+ return (uint32x4_t) __a;
}
#define __GET_LOW(__TYPE) \
--- /dev/null
+/* Test vreinterpret_f64_* and vreinterpret_*_f64 intrinsics work correctly. */
+/* { dg-do run } */
+/* { dg-options "-O3" } */
+
+#include <arm_neon.h>
+
+extern void abort (void);
+
+#define ABS(a) __builtin_fabs (a)
+#define ISNAN(a) __builtin_isnan (a)
+
+#define DOUBLE_EQUALS(a, b, epsilon) \
+( \
+ ((a) == (b)) \
+ || (ISNAN (a) && ISNAN (b)) \
+ || (ABS (a - b) < epsilon) \
+)
+
+/* Pi accurate up to 16 digits.
+ Further digits are a closest binary approximation. */
+#define PI_F64 3.14159265358979311599796346854
+/* Hex representation in Double (IEEE754 Double precision 64-bit) is:
+ 0x400921FB54442D18. */
+
+/* E accurate up to 16 digits.
+ Further digits are a closest binary approximation. */
+#define E_F64 2.71828182845904509079559829843
+/* Hex representation in Double (IEEE754 Double precision 64-bit) is:
+ 0x4005BF0A8B145769. */
+
+float32x2_t __attribute__ ((noinline))
+wrap_vreinterpret_f32_f64 (float64x1_t __a)
+{
+ return vreinterpret_f32_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_f32_f64 ()
+{
+ float64x1_t a;
+ float32x2_t b;
+ float64_t c[1] = { PI_F64 };
+ /* Values { 0x54442D18, 0x400921FB } reinterpreted as f32. */
+ float32_t d[2] = { 3.3702805504E12, 2.1426990032196044921875E0 };
+ float32_t e[2];
+ int i;
+
+ a = vld1_f64 (c);
+ b = wrap_vreinterpret_f32_f64 (a);
+ vst1_f32 (e, b);
+ for (i = 0; i < 2; i++)
+ if (!DOUBLE_EQUALS (d[i], e[i], __FLT_EPSILON__))
+ return 1;
+ return 0;
+};
+
+int8x8_t __attribute__ ((noinline))
+wrap_vreinterpret_s8_f64 (float64x1_t __a)
+{
+ return vreinterpret_s8_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_s8_f64 ()
+{
+ float64x1_t a;
+ int8x8_t b;
+ float64_t c[1] = { PI_F64 };
+ int8_t d[8] = { 0x18, 0x2D, 0x44, 0x54, 0xFB, 0x21, 0x09, 0x40 };
+ int8_t e[8];
+ int i;
+
+ a = vld1_f64 (c);
+ b = wrap_vreinterpret_s8_f64 (a);
+ vst1_s8 (e, b);
+ for (i = 0; i < 8; i++)
+ if (d[i] != e[i])
+ return 1;
+ return 0;
+};
+
+int16x4_t __attribute__ ((noinline))
+wrap_vreinterpret_s16_f64 (float64x1_t __a)
+{
+ return vreinterpret_s16_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_s16_f64 ()
+{
+ float64x1_t a;
+ int16x4_t b;
+ float64_t c[1] = { PI_F64 };
+ int16_t d[4] = { 0x2D18, 0x5444, 0x21FB, 0x4009 };
+ int16_t e[4];
+ int i;
+
+ a = vld1_f64 (c);
+ b = wrap_vreinterpret_s16_f64 (a);
+ vst1_s16 (e, b);
+ for (i = 0; i < 4; i++)
+ if (d[i] != e[i])
+ return 1;
+ return 0;
+};
+
+int32x2_t __attribute__ ((noinline))
+wrap_vreinterpret_s32_f64 (float64x1_t __a)
+{
+ return vreinterpret_s32_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_s32_f64 ()
+{
+ float64x1_t a;
+ int32x2_t b;
+ float64_t c[1] = { PI_F64 };
+ int32_t d[2] = { 0x54442D18, 0x400921FB };
+ int32_t e[2];
+ int i;
+
+ a = vld1_f64 (c);
+ b = wrap_vreinterpret_s32_f64 (a);
+ vst1_s32 (e, b);
+ for (i = 0; i < 2; i++)
+ if (d[i] != e[i])
+ return 1;
+ return 0;
+};
+
+int64x1_t __attribute__ ((noinline))
+wrap_vreinterpret_s64_f64 (float64x1_t __a)
+{
+ return vreinterpret_s64_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_s64_f64 ()
+{
+ float64x1_t a;
+ int64x1_t b;
+ float64_t c[1] = { PI_F64 };
+ int64_t d[1] = { 0x400921FB54442D18 };
+ int64_t e[1];
+ int i;
+
+ a = vld1_f64 (c);
+ b = wrap_vreinterpret_s64_f64 (a);
+ vst1_s64 (e, b);
+ if (d[0] != e[0])
+ return 1;
+ return 0;
+};
+
+float32x4_t __attribute__ ((noinline))
+wrap_vreinterpretq_f32_f64 (float64x2_t __a)
+{
+ return vreinterpretq_f32_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_f32_f64 ()
+{
+ float64x2_t a;
+ float32x4_t b;
+ float64_t c[2] = { PI_F64, E_F64 };
+
+ /* Values corresponding to f32 reinterpret of
+ { 0x54442D18, 0x400921FB, 0x8B145769, 0x4005BF0A }. */
+ float32_t d[4] = { 3.3702805504E12,
+ 2.1426990032196044921875E0,
+ -2.8569523269651966444143014594E-32,
+ 2.089785099029541015625E0 };
+ float32_t e[4];
+ int i;
+
+ a = vld1q_f64 (c);
+ b = wrap_vreinterpretq_f32_f64 (a);
+ vst1q_f32 (e, b);
+ for (i = 0; i < 4; i++)
+ {
+ if (!DOUBLE_EQUALS (d[i], e[i], __FLT_EPSILON__))
+ return 1;
+ }
+ return 0;
+};
+
+int8x16_t __attribute__ ((noinline))
+wrap_vreinterpretq_s8_f64 (float64x2_t __a)
+{
+ return vreinterpretq_s8_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_s8_f64 ()
+{
+ float64x2_t a;
+ int8x16_t b;
+ float64_t c[2] = { PI_F64, E_F64 };
+ int8_t d[16] = { 0x18, 0x2D, 0x44, 0x54, 0xFB, 0x21, 0x09, 0x40,
+ 0x69, 0x57, 0x14, 0x8B, 0x0A, 0xBF, 0x05, 0x40 };
+ int8_t e[16];
+ int i;
+
+ a = vld1q_f64 (c);
+ b = wrap_vreinterpretq_s8_f64 (a);
+ vst1q_s8 (e, b);
+ for (i = 0; i < 16; i++)
+ if (d[i] != e[i])
+ return 1;
+ return 0;
+};
+
+int16x8_t __attribute__ ((noinline))
+wrap_vreinterpretq_s16_f64 (float64x2_t __a)
+{
+ return vreinterpretq_s16_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_s16_f64 ()
+{
+ float64x2_t a;
+ int16x8_t b;
+ float64_t c[2] = { PI_F64, E_F64 };
+ int16_t d[8] = { 0x2D18, 0x5444, 0x21FB, 0x4009,
+ 0x5769, 0x8B14, 0xBF0A, 0x4005 };
+ int16_t e[8];
+ int i;
+
+ a = vld1q_f64 (c);
+ b = wrap_vreinterpretq_s16_f64 (a);
+ vst1q_s16 (e, b);
+ for (i = 0; i < 8; i++)
+ if (d[i] != e[i])
+ return 1;
+ return 0;
+};
+
+int32x4_t __attribute__ ((noinline))
+wrap_vreinterpretq_s32_f64 (float64x2_t __a)
+{
+ return vreinterpretq_s32_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_s32_f64 ()
+{
+ float64x2_t a;
+ int32x4_t b;
+ float64_t c[2] = { PI_F64, E_F64 };
+ int32_t d[4] = { 0x54442D18, 0x400921FB, 0x8B145769, 0x4005BF0A };
+ int32_t e[4];
+ int i;
+
+ a = vld1q_f64 (c);
+ b = wrap_vreinterpretq_s32_f64 (a);
+ vst1q_s32 (e, b);
+ for (i = 0; i < 4; i++)
+ if (d[i] != e[i])
+ return 1;
+ return 0;
+};
+
+int64x2_t __attribute__ ((noinline))
+wrap_vreinterpretq_s64_f64 (float64x2_t __a)
+{
+ return vreinterpretq_s64_f64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_s64_f64 ()
+{
+ float64x2_t a;
+ int64x2_t b;
+ float64_t c[2] = { PI_F64, E_F64 };
+ int64_t d[2] = { 0x400921FB54442D18, 0x4005BF0A8B145769 };
+ int64_t e[2];
+ int i;
+
+ a = vld1q_f64 (c);
+ b = wrap_vreinterpretq_s64_f64 (a);
+ vst1q_s64 (e, b);
+ for (i = 0; i < 2; i++)
+ if (d[i] != e[i])
+ return 1;
+ return 0;
+};
+
+float64x1_t __attribute__ ((noinline))
+wrap_vreinterpret_f64_f32 (float32x2_t __a)
+{
+ return vreinterpret_f64_f32 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_f64_f32 ()
+{
+ float32x2_t a;
+ float64x1_t b;
+ /* Values { 0x54442D18, 0x400921FB } reinterpreted as f32. */
+ float32_t c[2] = { 3.3702805504E12, 2.1426990032196044921875E0 };
+ float64_t d[1] = { PI_F64 };
+ float64_t e[1];
+ int i;
+
+ a = vld1_f32 (c);
+ b = wrap_vreinterpret_f64_f32 (a);
+ vst1_f64 (e, b);
+ if (!DOUBLE_EQUALS (d[0], e[0], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x1_t __attribute__ ((noinline))
+wrap_vreinterpret_f64_s8 (int8x8_t __a)
+{
+ return vreinterpret_f64_s8 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_f64_s8 ()
+{
+ int8x8_t a;
+ float64x1_t b;
+ int8_t c[8] = { 0x18, 0x2D, 0x44, 0x54, 0xFB, 0x21, 0x09, 0x40 };
+ float64_t d[1] = { PI_F64 };
+ float64_t e[1];
+ int i;
+
+ a = vld1_s8 (c);
+ b = wrap_vreinterpret_f64_s8 (a);
+ vst1_f64 (e, b);
+ if (!DOUBLE_EQUALS (d[0], e[0], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x1_t __attribute__ ((noinline))
+wrap_vreinterpret_f64_s16 (int16x4_t __a)
+{
+ return vreinterpret_f64_s16 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_f64_s16 ()
+{
+ int16x4_t a;
+ float64x1_t b;
+ int16_t c[4] = { 0x2D18, 0x5444, 0x21FB, 0x4009 };
+ float64_t d[1] = { PI_F64 };
+ float64_t e[1];
+ int i;
+
+ a = vld1_s16 (c);
+ b = wrap_vreinterpret_f64_s16 (a);
+ vst1_f64 (e, b);
+ if (!DOUBLE_EQUALS (d[0], e[0], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x1_t __attribute__ ((noinline))
+wrap_vreinterpret_f64_s32 (int32x2_t __a)
+{
+ return vreinterpret_f64_s32 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_f64_s32 ()
+{
+ int32x2_t a;
+ float64x1_t b;
+ int32_t c[2] = { 0x54442D18, 0x400921FB };
+ float64_t d[1] = { PI_F64 };
+ float64_t e[1];
+ int i;
+
+ a = vld1_s32 (c);
+ b = wrap_vreinterpret_f64_s32 (a);
+ vst1_f64 (e, b);
+ if (!DOUBLE_EQUALS (d[0], e[0], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x1_t __attribute__ ((noinline))
+wrap_vreinterpret_f64_s64 (int64x1_t __a)
+{
+ return vreinterpret_f64_s64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpret_f64_s64 ()
+{
+ int64x1_t a;
+ float64x1_t b;
+ int64_t c[1] = { 0x400921FB54442D18 };
+ float64_t d[1] = { PI_F64 };
+ float64_t e[1];
+
+ a = vld1_s64 (c);
+ b = wrap_vreinterpret_f64_s64 (a);
+ vst1_f64 (e, b);
+ if (!DOUBLE_EQUALS (d[0], e[0], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x2_t __attribute__ ((noinline))
+wrap_vreinterpretq_f64_f32 (float32x4_t __a)
+{
+ return vreinterpretq_f64_f32 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_f64_f32 ()
+{
+ float32x4_t a;
+ float64x2_t b;
+ /* Values corresponding to f32 reinterpret of
+ { 0x54442D18, 0x400921FB, 0x8B145769, 0x4005BF0A }. */
+ float32_t c[4] = { 3.3702805504E12,
+ 2.1426990032196044921875E0,
+ -2.8569523269651966444143014594E-32,
+ 2.089785099029541015625E0 };
+
+ float64_t d[2] = { PI_F64, E_F64 };
+ float64_t e[2];
+ int i;
+
+ a = vld1q_f32 (c);
+ b = wrap_vreinterpretq_f64_f32 (a);
+ vst1q_f64 (e, b);
+ for (i = 0; i < 2; i++)
+ if (!DOUBLE_EQUALS (d[i], e[i], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x2_t __attribute__ ((noinline))
+wrap_vreinterpretq_f64_s8 (int8x16_t __a)
+{
+ return vreinterpretq_f64_s8 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_f64_s8 ()
+{
+ int8x16_t a;
+ float64x2_t b;
+ int8_t c[16] = { 0x18, 0x2D, 0x44, 0x54, 0xFB, 0x21, 0x09, 0x40,
+ 0x69, 0x57, 0x14, 0x8B, 0x0A, 0xBF, 0x05, 0x40 };
+ float64_t d[2] = { PI_F64, E_F64 };
+ float64_t e[2];
+ int i;
+
+ a = vld1q_s8 (c);
+ b = wrap_vreinterpretq_f64_s8 (a);
+ vst1q_f64 (e, b);
+ for (i = 0; i < 2; i++)
+ if (!DOUBLE_EQUALS (d[i], e[i], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x2_t __attribute__ ((noinline))
+wrap_vreinterpretq_f64_s16 (int16x8_t __a)
+{
+ return vreinterpretq_f64_s16 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_f64_s16 ()
+{
+ int16x8_t a;
+ float64x2_t b;
+ int16_t c[8] = { 0x2D18, 0x5444, 0x21FB, 0x4009,
+ 0x5769, 0x8B14, 0xBF0A, 0x4005 };
+ float64_t d[2] = { PI_F64, E_F64 };
+ float64_t e[2];
+ int i;
+
+ a = vld1q_s16 (c);
+ b = wrap_vreinterpretq_f64_s16 (a);
+ vst1q_f64 (e, b);
+ for (i = 0; i < 2; i++)
+ if (!DOUBLE_EQUALS (d[i], e[i], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x2_t __attribute__ ((noinline))
+wrap_vreinterpretq_f64_s32 (int32x4_t __a)
+{
+ return vreinterpretq_f64_s32 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_f64_s32 ()
+{
+ int32x4_t a;
+ float64x2_t b;
+ int32_t c[4] = { 0x54442D18, 0x400921FB, 0x8B145769, 0x4005BF0A };
+ float64_t d[2] = { PI_F64, E_F64 };
+ float64_t e[2];
+ int i;
+
+ a = vld1q_s32 (c);
+ b = wrap_vreinterpretq_f64_s32 (a);
+ vst1q_f64 (e, b);
+ for (i = 0; i < 2; i++)
+ if (!DOUBLE_EQUALS (d[i], e[i], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+float64x2_t __attribute__ ((noinline))
+wrap_vreinterpretq_f64_s64 (int64x2_t __a)
+{
+ return vreinterpretq_f64_s64 (__a);
+}
+
+int __attribute__ ((noinline))
+test_vreinterpretq_f64_s64 ()
+{
+ int64x2_t a;
+ float64x2_t b;
+ int64_t c[2] = { 0x400921FB54442D18, 0x4005BF0A8B145769 };
+ float64_t d[2] = { PI_F64, E_F64 };
+ float64_t e[2];
+ int i;
+
+ a = vld1q_s64 (c);
+ b = wrap_vreinterpretq_f64_s64 (a);
+ vst1q_f64 (e, b);
+ for (i = 0; i < 2; i++)
+ if (!DOUBLE_EQUALS (d[i], e[i], __DBL_EPSILON__))
+ return 1;
+ return 0;
+};
+
+int
+main (int argc, char **argv)
+{
+ if (test_vreinterpret_f32_f64 ())
+ abort ();
+
+ if (test_vreinterpret_s8_f64 ())
+ abort ();
+ if (test_vreinterpret_s16_f64 ())
+ abort ();
+ if (test_vreinterpret_s32_f64 ())
+ abort ();
+ if (test_vreinterpret_s64_f64 ())
+ abort ();
+
+ if (test_vreinterpretq_f32_f64 ())
+ abort ();
+
+ if (test_vreinterpretq_s8_f64 ())
+ abort ();
+ if (test_vreinterpretq_s16_f64 ())
+ abort ();
+ if (test_vreinterpretq_s32_f64 ())
+ abort ();
+ if (test_vreinterpretq_s64_f64 ())
+ abort ();
+
+ if (test_vreinterpret_f64_f32 ())
+ abort ();
+
+ if (test_vreinterpret_f64_s8 ())
+ abort ();
+ if (test_vreinterpret_f64_s16 ())
+ abort ();
+ if (test_vreinterpret_f64_s32 ())
+ abort ();
+ if (test_vreinterpret_f64_s64 ())
+ abort ();
+
+ if (test_vreinterpretq_f64_f32 ())
+ abort ();
+
+ if (test_vreinterpretq_f64_s8 ())
+ abort ();
+ if (test_vreinterpretq_f64_s16 ())
+ abort ();
+ if (test_vreinterpretq_f64_s32 ())
+ abort ();
+ if (test_vreinterpretq_f64_s64 ())
+ abort ();
+
+ return 0;
+}
projects / platform / upstream / gcc49.git / commitdiff