| Message ID | 20240628052719.330451-2-hongtao.liu@intel.com |
|---|---|
| State | New |
| Headers | show |
| Series | Enable pass_late_combine for x86. | expand |
diff --git a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntb.c b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntb.c index 44b82c0519d..66d24107c26 100644 --- a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntb.c +++ b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntb.c @@ -7,10 +7,9 @@ #include <x86intrin.h> extern __m512i z, z1; - +extern __mmask16 msk; int foo () { - __mmask16 msk; __m512i c = _mm512_popcnt_epi8 (z); asm volatile ("" : "+v" (c)); c = _mm512_mask_popcnt_epi8 (z1, msk, z); diff --git a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntbvl.c b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntbvl.c index 8c2dfaba9c6..8ab05653f7c 100644 --- a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntbvl.c +++ b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntbvl.c @@ -11,11 +11,11 @@ extern __m256i y, y_1; extern __m128i x, x_1; +extern __mmask32 msk32; +extern __mmask16 msk16; int foo () { - __mmask32 msk32; - __mmask16 msk16; __m256i c256 = _mm256_popcnt_epi8 (y); asm volatile ("" : "+v" (c256)); c256 = _mm256_mask_popcnt_epi8 (y_1, msk32, y); diff --git a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntw.c b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntw.c index 2ef8589f6c1..c741bf48a51 100644 --- a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntw.c +++ b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntw.c @@ -7,10 +7,10 @@ #include <x86intrin.h> extern __m512i z, z1; +extern __mmask16 msk; int foo () { - __mmask16 msk; __m512i c = _mm512_popcnt_epi16 (z); asm volatile ("" : "+v" (c)); c = _mm512_mask_popcnt_epi16 (z1, msk, z); diff --git a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntwvl.c b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntwvl.c index c976461b12e..79bb3c31e85 100644 --- a/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntwvl.c +++ b/gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntwvl.c @@ -11,11 +11,11 @@ extern __m256i y, y_1; extern __m128i x, x_1; +extern __mmask16 msk16; +extern __mmask8 msk8; int foo () { - __mmask16 msk16; - __mmask8 msk8; __m256i c256 = _mm256_popcnt_epi16 (y); asm volatile ("" : "+v" (c256)); c256 = _mm256_mask_popcnt_epi16 (y_1, msk16, y); diff --git a/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntd.c b/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntd.c index b4d82f97032..776a4753d8e 100644 --- a/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntd.c +++ b/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntd.c @@ -15,11 +15,12 @@ extern __m128i x, x_1; extern __m256i y, y_1; extern __m512i z, z_1; +extern __mmask16 msk; +extern __mmask8 msk8; + int foo () { - __mmask16 msk; - __mmask8 msk8; __m128i a = _mm_popcnt_epi32 (x); asm volatile ("" : "+v" (a)); a = _mm_mask_popcnt_epi32 (x_1, msk8, x); diff --git a/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntq.c b/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntq.c index e87d6c999b6..c6314ac5deb 100644 --- a/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntq.c +++ b/gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntq.c @@ -15,10 +15,10 @@ extern __m128i x, x_1; extern __m256i y, y_1; extern __m512i z, z_1; +extern __mmask8 msk; int foo () { - __mmask8 msk; __m128i a = _mm_popcnt_epi64 (x); asm volatile ("" : "+v" (a)); a = _mm_mask_popcnt_epi64 (x_1, msk, x);
The testcases are supposed to scan for vpopcnt{b,w,d,q} operations with k mask, but mask is defined as uninitialized local variable which will be set as 0 at rtl expand phase. And it's further simplified off by late_combine which caused scan assembly failure. Move the definition of mask outside to make the testcases more stable. gcc/testsuite/ChangeLog: PR target/115610 * gcc.target/i386/avx512bitalg-vpopcntb.c: Define mask as extern instead of uninitialized local variables. * gcc.target/i386/avx512bitalg-vpopcntbvl.c: Ditto. * gcc.target/i386/avx512bitalg-vpopcntw.c: Ditto. * gcc.target/i386/avx512bitalg-vpopcntwvl.c: Ditto. * gcc.target/i386/avx512vpopcntdq-vpopcntd.c: Ditto. * gcc.target/i386/avx512vpopcntdq-vpopcntq.c: Ditto. --- gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntb.c | 3 +-- gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntbvl.c | 4 ++-- gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntw.c | 2 +- gcc/testsuite/gcc.target/i386/avx512bitalg-vpopcntwvl.c | 4 ++-- gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntd.c | 5 +++-- gcc/testsuite/gcc.target/i386/avx512vpopcntdq-vpopcntq.c | 2 +- 6 files changed, 10 insertions(+), 10 deletions(-)