Hi All,
The iterators ANY64 and ANY128 are used in various general split patterns and
are supposed to contain any 64 bit and 128 bit modes respectively.
For some reason these patterns had HI but not HF. This adds HF so that general
64 and 128 bit splits are generated for these modes as well. These are required
by various split patterns that expect them to be there.
Bootstrapped Regtested on aarch64-none-linux-gnu and <native regtest still
running> issues.
Ok for trunk?
Thanks,
Tamar
gcc/ChangeLog:
2019-02-13 Tamar Christina <tamar.christ...@arm.com>
PR target/88850
* config/arm/iterators.md (ANY64): Add V4HF,
(ANY128): Add V8HF.
gcc/testsuite/ChangeLog:
2019-02-13 Tamar Christina <tamar.christ...@arm.com>
PR target/88850
* gcc.target/arm/pr88850-2.c: New test.
--
diff --git a/gcc/config/arm/iterators.md b/gcc/config/arm/iterators.md
index c33e572c3e89c3dc5848bd6b825d618481247558..4ac048a0c609273691c264c97ccf6cd47b43943b 100644
--- a/gcc/config/arm/iterators.md
+++ b/gcc/config/arm/iterators.md
@@ -24,11 +24,11 @@
;;----------------------------------------------------------------------------
;; A list of modes that are exactly 64 bits in size. This is used to expand
-;; some splits that are the same for all modes when operating on ARM
+;; some splits that are the same for all modes when operating on ARM
;; registers.
-(define_mode_iterator ANY64 [DI DF V8QI V4HI V2SI V2SF])
+(define_mode_iterator ANY64 [DI DF V8QI V4HI V4HF V2SI V2SF])
-(define_mode_iterator ANY128 [V2DI V2DF V16QI V8HI V4SI V4SF])
+(define_mode_iterator ANY128 [V2DI V2DF V16QI V8HI V8HF V4SI V4SF])
;; A list of integer modes that are up to one word long
(define_mode_iterator QHSI [QI HI SI])
diff --git a/gcc/testsuite/gcc.target/arm/pr88850-2.c b/gcc/testsuite/gcc.target/arm/pr88850-2.c
new file mode 100644
index 0000000000000000000000000000000000000000..fee2a0fe3a227ea4652bea2aa0e7335d20a7e9b5
--- /dev/null
+++ b/gcc/testsuite/gcc.target/arm/pr88850-2.c
@@ -0,0 +1,19 @@
+/* PR target/88850. */
+/* { dg-do compile } */
+/* { dg-additional-options "-O2 -march=armv7-a -mfloat-abi=softfp -fdump-rtl-final" } */
+/* { dg-add-options arm_neon_fp16 } */
+/* { dg-require-effective-target arm_soft_ok } */
+/* { dg-require-effective-target arm_neon_fp16_ok } */
+
+#include <arm_neon.h>
+
+extern void c (int, float16x4_t);
+
+void a (float16x4_t b)
+{
+ c (0, b);
+}
+
+
+/* Check that these 64-bit moves are done in SI. */
+/* { dg-final { scan-rtl-dump "_movsi_vfp" "final" } } */
