Hi!
These patterns printed bogus <>s around the {1to16} and similar strings.
Fixed thusly, bootstrapped/regtested on x86_64-linux and i686-linux,
committed to trunk as obvious. Will do backports momentarily.
2020-09-15 Jakub Jelinek <ja...@redhat.com>
PR target/97028
* config/i386/sse.md (*mul<mode>3<mask_name>_bcs,
*<avx512>_div<mode>3<mask_name>_bcst): Use <avx512bcst> instead of
<<avx512bcst>>.
* gcc.target/i386/avx512f-pr97028.c: Untested fix.
--- gcc/config/i386/sse.md.jj 2020-09-12 13:36:42.000000000 +0200
+++ gcc/config/i386/sse.md 2020-09-14 09:21:53.378315534 +0200
@@ -1867,7 +1867,7 @@ (define_insn "*mul<mode>3<mask_name>_bcs
(match_operand:<ssescalarmode> 1 "memory_operand" "m"))
(match_operand:VF_AVX512 2 "register_operand" "v")))]
"TARGET_AVX512F && <mask_mode512bit_condition>"
- "vmul<ssemodesuffix>\t{%1<avx512bcst>, %2,
%0<mask_operand3>|%0<mask_operand3>, %2, %1<<avx512bcst>>}"
+ "vmul<ssemodesuffix>\t{%1<avx512bcst>, %2,
%0<mask_operand3>|%0<mask_operand3>, %2, %1<avx512bcst>}"
[(set_attr "prefix" "evex")
(set_attr "type" "ssemul")
(set_attr "mode" "<MODE>")])
@@ -1960,7 +1960,7 @@ (define_insn "*<avx512>_div<mode>3<mask_
(vec_duplicate:VF_AVX512
(match_operand:<ssescalarmode> 2 "memory_operand" "m"))))]
"TARGET_AVX512F && <mask_mode512bit_condition>"
- "vdiv<ssemodesuffix>\t{%2<avx512bcst>, %1,
%0<mask_operand3>|%0<mask_operand3>, %1, %2<<avx512bcst>>}"
+ "vdiv<ssemodesuffix>\t{%2<avx512bcst>, %1,
%0<mask_operand3>|%0<mask_operand3>, %1, %2<avx512bcst>}"
[(set_attr "prefix" "evex")
(set_attr "type" "ssediv")
(set_attr "mode" "<MODE>")])
--- gcc/testsuite/gcc.target/i386/avx512f-pr97028.c.jj 2020-09-14
09:38:13.522659890 +0200
+++ gcc/testsuite/gcc.target/i386/avx512f-pr97028.c 2020-09-14
09:37:36.952206164 +0200
@@ -0,0 +1,18 @@
+/* PR target/97028 */
+/* { dg-do assemble { target avx512f } } */
+/* { dg-require-effective-target masm_intel } */
+/* { dg-options "-O2 -mavx512f -masm=intel" } */
+
+#include <x86intrin.h>
+
+__m512
+foo (__m512 x, float *y)
+{
+ return _mm512_mul_ps (x, _mm512_set1_ps (*y));
+}
+
+__m512
+bar (__m512 x, float *y)
+{
+ return _mm512_div_ps (x, _mm512_set1_ps (*y));
+}
Jakub
