Fix broken commit from r143594.
authorPaul Brook <pbrook@gcc.gnu.org>
Tue, 27 Jan 2009 16:14:13 +0000 (16:14 +0000)
committerPaul Brook <pbrook@gcc.gnu.org>
Tue, 27 Jan 2009 16:14:13 +0000 (16:14 +0000)
From-SVN: r143705

gcc/config.gcc
gcc/testsuite/gcc.target/arm/neon-cond-1.c [new file with mode: 0644]

index 63bd62bb6532de79a47b9058f3dcbbd011ff0922..aa224ae59df1fe1a35e6822d55a6a672ae96eef8 100644 (file)
@@ -760,7 +760,7 @@ arm*-*-eabi* | arm*-*-symbianelf* )
        tmake_file="arm/t-arm arm/t-arm-elf"
        case ${target} in
        arm*-*-eabi*)
-         tm_file="$tm_file arm/eabi.h arm/nocrt0.h"
+         tm_file="$tm_file arm/eabi.h"
          tmake_file="${tmake_file} arm/t-bpabi"
          extra_options="${extra_options} arm/eabi.opt"
          ;;
diff --git a/gcc/testsuite/gcc.target/arm/neon-cond-1.c b/gcc/testsuite/gcc.target/arm/neon-cond-1.c
new file mode 100644 (file)
index 0000000..7d87b6e
--- /dev/null
@@ -0,0 +1,30 @@
+/* { dg-do run } */
+/* { dg-require-effective-target arm_neon_hw } */
+/* { dg-options "-O2 -mfpu=neon -mfloat-abi=softfp" } */
+/* Check that the arm_final_prescan_insn ccfsm code does not try to
+ * conditionally execute NEON instructions.  */
+#include <arm_neon.h>
+#include <stdlib.h>
+
+int __attribute__((noinline))
+foo(uint32x2_t a, uint32_t *p, uint32_t *q)
+{
+  if (p != q)
+    /* This vst1 instruction could be conditional, except that NEON
+       instructions are never conditional in ARM mode.  */
+    vst1_u32(p, a);
+  return 0;
+}
+
+int
+main()
+{
+    uint32x2_t v;
+    uint32_t a[2] = {1, 42};
+    v = vld1_u32(a);
+    v = vadd_u32(v, v);
+    foo(v, a, a);
+    if (a[0] != 1 || a[1] != 42)
+      abort();
+    exit(0);
+}