diff options
| author | liuhongt <hongtao.liu@intel.com> | 2023-06-26 13:59:29 +0800 |
|---|---|---|
| committer | liuhongt <hongtao.liu@intel.com> | 2023-06-27 14:13:05 +0800 |
| commit | a90f558bbb87c0b5d2b1e07d55bd585b2285cf3d (patch) | |
| tree | 97db22da46efbed2ebe48f13ab79c298935533cf /gcc | |
| parent | fb909bc101f2dc7453e0ed187933e39acbab1b21 (diff) | |
| download | gcc-a90f558bbb87c0b5d2b1e07d55bd585b2285cf3d.zip gcc-a90f558bbb87c0b5d2b1e07d55bd585b2285cf3d.tar.gz gcc-a90f558bbb87c0b5d2b1e07d55bd585b2285cf3d.tar.bz2 | |
Don't issue vzeroupper for vzeroupper call_insn.
gcc/ChangeLog:
PR target/82735
* config/i386/i386.cc (ix86_avx_u127_mode_needed): Don't emit
vzeroupper for vzeroupper call_insn.
gcc/testsuite/ChangeLog:
* gcc.target/i386/avx-vzeroupper-30.c: New test.
Diffstat (limited to 'gcc')
| -rw-r--r-- | gcc/config/i386/i386.cc | 5 | ||||
| -rw-r--r-- | gcc/testsuite/gcc.target/i386/avx-vzeroupper-30.c | 15 |
2 files changed, 18 insertions, 2 deletions
diff --git a/gcc/config/i386/i386.cc b/gcc/config/i386/i386.cc index 0761965..caca74d 100644 --- a/gcc/config/i386/i386.cc +++ b/gcc/config/i386/i386.cc @@ -14489,8 +14489,9 @@ ix86_avx_u128_mode_needed (rtx_insn *insn) modes wider than 256 bits. It's only safe to issue a vzeroupper if all SSE registers are clobbered. */ const function_abi &abi = insn_callee_abi (insn); - if (!hard_reg_set_subset_p (reg_class_contents[SSE_REGS], - abi.mode_clobbers (V4DImode))) + if (vzeroupper_pattern (PATTERN (insn), VOIDmode) + || !hard_reg_set_subset_p (reg_class_contents[SSE_REGS], + abi.mode_clobbers (V4DImode))) return AVX_U128_ANY; return AVX_U128_CLEAN; diff --git a/gcc/testsuite/gcc.target/i386/avx-vzeroupper-30.c b/gcc/testsuite/gcc.target/i386/avx-vzeroupper-30.c new file mode 100644 index 0000000..c1c9baa --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/avx-vzeroupper-30.c @@ -0,0 +1,15 @@ +/* { dg-do compile } */ +/* { dg-options "-O2 -mavx -mvzeroupper -dp" } */ + +#include <immintrin.h> + +extern __m256 x, y; + +void +foo () +{ + x = y; + _mm256_zeroupper (); +} + +/* { dg-final { scan-assembler-times "avx_vzeroupper" 1 } } */ |