public inbox for gcc-bugs@sourceware.org
help / color / mirror / Atom feed
* [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel
@ 2020-09-12 0:38 nikita.shulga at gmail dot com
2020-09-12 0:44 ` [Bug target/97028] " nikita.shulga at gmail dot com
` (8 more replies)
0 siblings, 9 replies; 10+ messages in thread
From: nikita.shulga at gmail dot com @ 2020-09-12 0:38 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
Bug ID: 97028
Summary: Compilation errors for AVX512 intrinsic with
-masm=intel
Product: gcc
Version: 9.0
Status: UNCONFIRMED
Severity: normal
Priority: P3
Component: target
Assignee: unassigned at gcc dot gnu.org
Reporter: nikita.shulga at gmail dot com
Target Milestone: ---
Following code snippet, containing no asm blocks can be compiled just fine with
'-Os -mavx512f' options, by compilation fails using gcc-9.0 or newer if
'-masm=intel' is added：
#include <immintrin.h>
float foo(float* con) {
__mmask16 msk = 0x00ff;
__m512 a = _mm512_maskz_loadu_ps(msk, con);
__m512 b = _mm512_set1_ps(con[1]);
__m512 c = _mm512_mul_ps(a,b);
return ((float *)&c)[0];
}
That is:
$ gcc -c -Os -mavx512f mul.c ; echo $?
0
$ gcc -c -Os -masm=intel -mavx512f mul.c ; echo $?
/tmp/ccmeN1OP.s: Assembler messages:
/tmp/ccmeN1OP.s:12: Error: invalid use of register
1
And the offending instruction looks as follows:
$ gcc -S -o - -Os -masm=intel -mavx512f mul.c|head -n 12|tail -n1
vmulps zmm0, zmm0, DWORD PTR [rdi+4]<{1to16}>
But compilation works just fine if gcc-8 is used instead.
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
@ 2020-09-12 0:44 ` nikita.shulga at gmail dot com
2020-09-14 7:10 ` rguenth at gcc dot gnu.org
` (7 subsequent siblings)
8 siblings, 0 replies; 10+ messages in thread
From: nikita.shulga at gmail dot com @ 2020-09-12 0:44 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
--- Comment #1 from Nikita <nikita.shulga at gmail dot com> ---
Here is the link demonstrating the issue on https://godbolt.org/z/bc6669
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
2020-09-12 0:44 ` [Bug target/97028] " nikita.shulga at gmail dot com
@ 2020-09-14 7:10 ` rguenth at gcc dot gnu.org
2020-09-14 7:25 ` [Bug target/97028] [9/10/11 Regression] " jakub at gcc dot gnu.org
` (6 subsequent siblings)
8 siblings, 0 replies; 10+ messages in thread
From: rguenth at gcc dot gnu.org @ 2020-09-14 7:10 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
Richard Biener <rguenth at gcc dot gnu.org> changed:
What |Removed |Added
----------------------------------------------------------------------------
Ever confirmed|0 |1
Status|UNCONFIRMED |WAITING
Last reconfirmed| |2020-09-14
--- Comment #2 from Richard Biener <rguenth at gcc dot gnu.org> ---
it works for me, what assembler version are you using? I'm using gas 2.34.0
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] [9/10/11 Regression] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
2020-09-12 0:44 ` [Bug target/97028] " nikita.shulga at gmail dot com
2020-09-14 7:10 ` rguenth at gcc dot gnu.org
@ 2020-09-14 7:25 ` jakub at gcc dot gnu.org
2020-09-14 7:29 ` jakub at gcc dot gnu.org
` (5 subsequent siblings)
8 siblings, 0 replies; 10+ messages in thread
From: jakub at gcc dot gnu.org @ 2020-09-14 7:25 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
Jakub Jelinek <jakub at gcc dot gnu.org> changed:
What |Removed |Added
----------------------------------------------------------------------------
Summary|Compilation errors for |[9/10/11 Regression]
|AVX512 intrinsic with |Compilation errors for
|-masm=intel |AVX512 intrinsic with
| |-masm=intel
Target Milestone|--- |9.4
Assignee|unassigned at gcc dot gnu.org |jakub at gcc dot gnu.org
Status|WAITING |ASSIGNED
CC| |jakub at gcc dot gnu.org
--- Comment #3 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
I can reproduce it.
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] [9/10/11 Regression] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
` (2 preceding siblings ...)
2020-09-14 7:25 ` [Bug target/97028] [9/10/11 Regression] " jakub at gcc dot gnu.org
@ 2020-09-14 7:29 ` jakub at gcc dot gnu.org
2020-09-14 7:47 ` jakub at gcc dot gnu.org
` (4 subsequent siblings)
8 siblings, 0 replies; 10+ messages in thread
From: jakub at gcc dot gnu.org @ 2020-09-14 7:29 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
--- Comment #4 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Introduced with r9-3563-gc038638ea9dfc75fac9559cdb035754af85960d0 and
r9-3560-gfda5d5e6e040d23e7e751a491097090b8f5ff58a
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] [9/10/11 Regression] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
` (3 preceding siblings ...)
2020-09-14 7:29 ` jakub at gcc dot gnu.org
@ 2020-09-14 7:47 ` jakub at gcc dot gnu.org
2020-09-15 7:40 ` cvs-commit at gcc dot gnu.org
` (3 subsequent siblings)
8 siblings, 0 replies; 10+ messages in thread
From: jakub at gcc dot gnu.org @ 2020-09-14 7:47 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
--- Comment #5 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Created attachment 49213
--> https://gcc.gnu.org/bugzilla/attachment.cgi?id=49213&action=edit
gcc11-pr97028.patch
Untested fix.
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] [9/10/11 Regression] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
` (4 preceding siblings ...)
2020-09-14 7:47 ` jakub at gcc dot gnu.org
@ 2020-09-15 7:40 ` cvs-commit at gcc dot gnu.org
2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
` (2 subsequent siblings)
8 siblings, 0 replies; 10+ messages in thread
From: cvs-commit at gcc dot gnu.org @ 2020-09-15 7:40 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
--- Comment #6 from CVS Commits <cvs-commit at gcc dot gnu.org> ---
The master branch has been updated by Jakub Jelinek <jakub@gcc.gnu.org>:
https://gcc.gnu.org/g:0f079e104a8d1994b6b47169a6b45737615eb2d7
commit r11-3201-g0f079e104a8d1994b6b47169a6b45737615eb2d7
Author: Jakub Jelinek <jakub@redhat.com>
Date: Tue Sep 15 09:37:48 2020 +0200
i386: Fix up vector mul and div with broadcasts in -masm=intel mode
These patterns printed bogus <>s around the {1to16} and similar strings.
2020-09-15 Jakub Jelinek <jakub@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.
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] [9/10/11 Regression] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
` (5 preceding siblings ...)
2020-09-15 7:40 ` cvs-commit at gcc dot gnu.org
@ 2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
2020-09-15 8:29 ` jakub at gcc dot gnu.org
8 siblings, 0 replies; 10+ messages in thread
From: cvs-commit at gcc dot gnu.org @ 2020-09-15 8:29 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
--- Comment #7 from CVS Commits <cvs-commit at gcc dot gnu.org> ---
The releases/gcc-10 branch has been updated by Jakub Jelinek
<jakub@gcc.gnu.org>:
https://gcc.gnu.org/g:55cd12c65ffa1e7c0bb36fd398f178d5d15d660f
commit r10-8765-g55cd12c65ffa1e7c0bb36fd398f178d5d15d660f
Author: Jakub Jelinek <jakub@redhat.com>
Date: Tue Sep 15 09:37:48 2020 +0200
i386: Fix up vector mul and div with broadcasts in -masm=intel mode
These patterns printed bogus <>s around the {1to16} and similar strings.
2020-09-15 Jakub Jelinek <jakub@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.
(cherry picked from commit 0f079e104a8d1994b6b47169a6b45737615eb2d7)
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] [9/10/11 Regression] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
` (6 preceding siblings ...)
2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
@ 2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
2020-09-15 8:29 ` jakub at gcc dot gnu.org
8 siblings, 0 replies; 10+ messages in thread
From: cvs-commit at gcc dot gnu.org @ 2020-09-15 8:29 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
--- Comment #8 from CVS Commits <cvs-commit at gcc dot gnu.org> ---
The releases/gcc-9 branch has been updated by Jakub Jelinek
<jakub@gcc.gnu.org>:
https://gcc.gnu.org/g:d0a094ce39fc49681b0d5cfd2ee1d232859c4824
commit r9-8871-gd0a094ce39fc49681b0d5cfd2ee1d232859c4824
Author: Jakub Jelinek <jakub@redhat.com>
Date: Tue Sep 15 09:37:48 2020 +0200
i386: Fix up vector mul and div with broadcasts in -masm=intel mode
These patterns printed bogus <>s around the {1to16} and similar strings.
2020-09-15 Jakub Jelinek <jakub@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.
(cherry picked from commit 0f079e104a8d1994b6b47169a6b45737615eb2d7)
^ permalink raw reply [flat|nested] 10+ messages in thread
* [Bug target/97028] [9/10/11 Regression] Compilation errors for AVX512 intrinsic with -masm=intel
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
` (7 preceding siblings ...)
2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
@ 2020-09-15 8:29 ` jakub at gcc dot gnu.org
8 siblings, 0 replies; 10+ messages in thread
From: jakub at gcc dot gnu.org @ 2020-09-15 8:29 UTC (permalink / raw)
To: gcc-bugs
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=97028
Jakub Jelinek <jakub at gcc dot gnu.org> changed:
What |Removed |Added
----------------------------------------------------------------------------
Status|ASSIGNED |RESOLVED
Resolution|--- |FIXED
--- Comment #9 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
Fixed for 9.4/10.3/11.1+.
^ permalink raw reply [flat|nested] 10+ messages in thread
end of thread, other threads:[~2020-09-15 8:29 UTC | newest]
Thread overview: 10+ messages (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2020-09-12 0:38 [Bug target/97028] New: Compilation errors for AVX512 intrinsic with -masm=intel nikita.shulga at gmail dot com
2020-09-12 0:44 ` [Bug target/97028] " nikita.shulga at gmail dot com
2020-09-14 7:10 ` rguenth at gcc dot gnu.org
2020-09-14 7:25 ` [Bug target/97028] [9/10/11 Regression] " jakub at gcc dot gnu.org
2020-09-14 7:29 ` jakub at gcc dot gnu.org
2020-09-14 7:47 ` jakub at gcc dot gnu.org
2020-09-15 7:40 ` cvs-commit at gcc dot gnu.org
2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
2020-09-15 8:29 ` cvs-commit at gcc dot gnu.org
2020-09-15 8:29 ` jakub at gcc dot gnu.org
This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for read-only IMAP folder(s) and NNTP newsgroup(s).