diff --git a/gcc/ChangeLog b/gcc/ChangeLog
index 14d19098562ec580cc9e9ae37b8a15addf5708cc..a2d97efa09249c2852692f825912a4b5ba45f656 100644
--- a/gcc/ChangeLog
+++ b/gcc/ChangeLog
@@ -1,3 +1,14 @@
+2014-07-01 Kyrylo Tkachov <kyrylo.tkachov@arm.com>
+
+ * config/aarch64/arm_neon.h (vcage_f64): New intrinsic.
+ (vcagt_f64): Likewise.
+ (vcale_f64): Likewise.
+ (vcaled_f64): Likewise.
+ (vcales_f32): Likewise.
+ (vcalt_f64): Likewise.
+ (vcaltd_f64): Likewise.
+ (vcalts_f32): Likewise.
+
2014-07-01 Marek Polacek <polacek@redhat.com>
* doc/invoke.texi: Document -Wint-conversion.
diff --git a/gcc/config/aarch64/arm_neon.h b/gcc/config/aarch64/arm_neon.h
index d5d8c23acd75b6f2a4e8cd6cc4daca418372f883..83ac5e96d422ceccadcb212ec792665b78c03fae 100644
--- a/gcc/config/aarch64/arm_neon.h
+++ b/gcc/config/aarch64/arm_neon.h
@@ -13823,6 +13823,12 @@ vaesimcq_u8 (uint8x16_t data)
/* vcage */
+__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
+vcage_f64 (float64x1_t __a, float64x1_t __b)
+{
+ return vabs_f64 (__a) >= vabs_f64 (__b);
+}
+
__extension__ static __inline uint32_t __attribute__ ((__always_inline__))
vcages_f32 (float32_t __a, float32_t __b)
{
@@ -13867,6 +13873,12 @@ vcagt_f32 (float32x2_t __a, float32x2_t __b)
return vabs_f32 (__a) > vabs_f32 (__b);
}
+__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
+vcagt_f64 (float64x1_t __a, float64x1_t __b)
+{
+ return vabs_f64 (__a) > vabs_f64 (__b);
+}
+
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vcagtq_f32 (float32x4_t __a, float32x4_t __b)
{
@@ -13893,6 +13905,24 @@ vcale_f32 (float32x2_t __a, float32x2_t __b)
return vabs_f32 (__a) <= vabs_f32 (__b);
}
+__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
+vcale_f64 (float64x1_t __a, float64x1_t __b)
+{
+ return vabs_f64 (__a) <= vabs_f64 (__b);
+}
+
+__extension__ static __inline uint64_t __attribute__ ((__always_inline__))
+vcaled_f64 (float64_t __a, float64_t __b)
+{
+ return __builtin_fabs (__a) <= __builtin_fabs (__b) ? -1 : 0;
+}
+
+__extension__ static __inline uint32_t __attribute__ ((__always_inline__))
+vcales_f32 (float32_t __a, float32_t __b)
+{
+ return __builtin_fabsf (__a) <= __builtin_fabsf (__b) ? -1 : 0;
+}
+
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vcaleq_f32 (float32x4_t __a, float32x4_t __b)
{
@@ -13913,6 +13943,18 @@ vcalt_f32 (float32x2_t __a, float32x2_t __b)
return vabs_f32 (__a) < vabs_f32 (__b);
}
+__extension__ static __inline uint64x1_t __attribute__ ((__always_inline__))
+vcalt_f64 (float64x1_t __a, float64x1_t __b)
+{
+ return vabs_f64 (__a) < vabs_f64 (__b);
+}
+
+__extension__ static __inline uint64_t __attribute__ ((__always_inline__))
+vcaltd_f64 (float64_t __a, float64_t __b)
+{
+ return __builtin_fabs (__a) < __builtin_fabs (__b) ? -1 : 0;
+}
+
__extension__ static __inline uint32x4_t __attribute__ ((__always_inline__))
vcaltq_f32 (float32x4_t __a, float32x4_t __b)
{
@@ -13925,6 +13967,12 @@ vcaltq_f64 (float64x2_t __a, float64x2_t __b)
return vabsq_f64 (__a) < vabsq_f64 (__b);
}
+__extension__ static __inline uint32_t __attribute__ ((__always_inline__))
+vcalts_f32 (float32_t __a, float32_t __b)
+{
+ return __builtin_fabsf (__a) < __builtin_fabsf (__b) ? -1 : 0;
+}
+
/* vceq - vector. */
__extension__ static __inline uint32x2_t __attribute__ ((__always_inline__))
diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog
index fd72e05320c15901f87ca437c81875070b8de433..e12393c9e59681b19f304a4fd3f464f4d68e6491 100644
--- a/gcc/testsuite/ChangeLog
+++ b/gcc/testsuite/ChangeLog
@@ -1,3 +1,14 @@
+2014-07-01 Kyrylo Tkachov <kyrylo.tkachov@arm.com>
+
+ * gcc.target/aarch64/simd/vcage_f64.c: New test.
+ * gcc.target/aarch64/simd/vcagt_f64.c: Likewise.
+ * gcc.target/aarch64/simd/vcale_f64.c: Likewise.
+ * gcc.target/aarch64/simd/vcaled_f64.c: Likewise.
+ * gcc.target/aarch64/simd/vcales_f32.c: Likewise.
+ * gcc.target/aarch64/simd/vcalt_f64.c: Likewise.
+ * gcc.target/aarch64/simd/vcaltd_f64.c: Likewise.
+ * gcc.target/aarch64/simd/vcalts_f32.c: Likewise.
+
2014-07-01 Paolo Carlini <paolo.carlini@oracle.com>
* g++.dg/cpp1y/pr59867.C: Fix target selector.
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcage_f64.c b/gcc/testsuite/gcc.target/aarch64/simd/vcage_f64.c
new file mode 100644
index 0000000000000000000000000000000000000000..7ddef58e4af8866549653909d33f7844d8e905f3
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcage_f64.c
@@ -0,0 +1,38 @@
+/* Test the vcage_f64 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float64_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint64_t expected;
+ uint64_t actual;
+ float64x1_t arg1, arg2;
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) >= __builtin_fabs (in[j]) ? -1 : 0;
+ arg1 = (float64x1_t) { in[i] };
+ arg2 = (float64x1_t) { in[j] };
+ actual = vget_lane_u64 (vcage_f64 (arg1, arg2), 0);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facge\[ \t\]+\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcagt_f64.c b/gcc/testsuite/gcc.target/aarch64/simd/vcagt_f64.c
new file mode 100644
index 0000000000000000000000000000000000000000..df6911a24894f55bc973c282e97809754639c22f
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcagt_f64.c
@@ -0,0 +1,38 @@
+/* Test the vcagt_f64 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float64_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint64_t expected;
+ uint64_t actual;
+ float64x1_t arg1, arg2;
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) > __builtin_fabs (in[j]) ? -1 : 0;
+ arg1 = (float64x1_t) { in[i] };
+ arg2 = (float64x1_t) { in[j] };
+ actual = vget_lane_u64 (vcagt_f64 (arg1, arg2), 0);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facgt\[ \t\]+\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcale_f64.c b/gcc/testsuite/gcc.target/aarch64/simd/vcale_f64.c
new file mode 100644
index 0000000000000000000000000000000000000000..574bfea1b7ae20269312b40ec797d851d993a273
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcale_f64.c
@@ -0,0 +1,38 @@
+/* Test the vcale_f64 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float64_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint64_t expected;
+ uint64_t actual;
+ float64x1_t arg1, arg2;
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) <= __builtin_fabs (in[j]) ? -1 : 0;
+ arg1 = (float64x1_t) { in[i] };
+ arg2 = (float64x1_t) { in[j] };
+ actual = vget_lane_u64 (vcale_f64 (arg1, arg2), 0);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facge\[ \t\]+\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcaled_f64.c b/gcc/testsuite/gcc.target/aarch64/simd/vcaled_f64.c
new file mode 100644
index 0000000000000000000000000000000000000000..9ea31d6c0fea5c6528cd0e1b39b6e35787589733
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcaled_f64.c
@@ -0,0 +1,36 @@
+/* Test the vcaled_f64 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float64_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint64_t expected;
+ uint64_t actual;
+
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) <= __builtin_fabs (in[j]) ? -1 : 0;
+ actual = vcaled_f64 (in[i], in[j]);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facge\[ \t\]+\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcales_f32.c b/gcc/testsuite/gcc.target/aarch64/simd/vcales_f32.c
new file mode 100644
index 0000000000000000000000000000000000000000..a69a096a7652bca68995af3daaa55710add9b7b2
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcales_f32.c
@@ -0,0 +1,36 @@
+/* Test the vcales_f32 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float32_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint32_t expected;
+ uint32_t actual;
+
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) <= __builtin_fabs (in[j]) ? -1 : 0;
+ actual = vcales_f32 (in[i], in[j]);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facge\[ \t\]+\[sS\]\[0-9\]+, ?\[sS\]\[0-9\]+, ?\[sS\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcalt_f64.c b/gcc/testsuite/gcc.target/aarch64/simd/vcalt_f64.c
new file mode 100644
index 0000000000000000000000000000000000000000..d5bf5f37ebabcb8af74fedd1e38597feb078c639
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcalt_f64.c
@@ -0,0 +1,38 @@
+/* Test the vcalt_f64 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float64_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint64_t expected;
+ uint64_t actual;
+ float64x1_t arg1, arg2;
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) < __builtin_fabs (in[j]) ? -1 : 0;
+ arg1 = (float64x1_t) { in[i] };
+ arg2 = (float64x1_t) { in[j] };
+ actual = vget_lane_u64 (vcalt_f64 (arg1, arg2), 0);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facgt\[ \t\]+\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcaltd_f64.c b/gcc/testsuite/gcc.target/aarch64/simd/vcaltd_f64.c
new file mode 100644
index 0000000000000000000000000000000000000000..fcdd75b6af78ddbb22251e9c6dbd289d6f6bcde7
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcaltd_f64.c
@@ -0,0 +1,36 @@
+/* Test the vcaltd_f64 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float64_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint64_t expected;
+ uint64_t actual;
+
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) < __builtin_fabs (in[j]) ? -1 : 0;
+ actual = vcaltd_f64 (in[i], in[j]);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facgt\[ \t\]+\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+, ?\[dD\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */
diff --git a/gcc/testsuite/gcc.target/aarch64/simd/vcalts_f32.c b/gcc/testsuite/gcc.target/aarch64/simd/vcalts_f32.c
new file mode 100644
index 0000000000000000000000000000000000000000..0799dd7486658d6353e28c006d69f741a4dec08e
--- /dev/null
+++ b/gcc/testsuite/gcc.target/aarch64/simd/vcalts_f32.c
@@ -0,0 +1,36 @@
+/* Test the vcalts_f32 AArch64 SIMD intrinsic. */
+
+/* { dg-do run } */
+/* { dg-options "-save-temps -O3" } */
+
+#include "arm_neon.h"
+
+#define SIZE 6
+
+extern void abort (void);
+
+volatile float32_t in[SIZE] = { -10.4, -3.14, 0.0, 1.5, 5.3, 532.3 };
+
+int
+main (void)
+{
+ uint32_t expected;
+ uint32_t actual;
+
+ int i, j;
+
+ for (i = 0; i < SIZE; ++i)
+ for (j = 0; j < SIZE; ++j)
+ {
+ expected = __builtin_fabs (in[i]) < __builtin_fabs (in[j]) ? -1 : 0;
+ actual = vcalts_f32 (in[i], in[j]);
+
+ if (actual != expected)
+ abort ();
+ }
+
+ return 0;
+}
+
+/* { dg-final { scan-assembler "facgt\[ \t\]+\[sS\]\[0-9\]+, ?\[sS\]\[0-9\]+, ?\[sS\]\[0-9\]+\n" } } */
+/* { dg-final { cleanup-saved-temps } } */