FreeChainXenon/gcc
1
0
Fork 0
Code Issues Pull requests Projects Releases Packages Wiki Activity Actions

re PR target/87853 (_mm_cmpgt_epi8 broken with -funsigned-char)

Browse source 
PR target/87853
	* config/i386/emmintrin.h (_mm_cmpeq_epi8): Use casts to __v16qi
	instead of __v16qs.

	* gcc.target/i386/pr87853.c: New test.

From-SVN: r275508
This commit is contained in:
Jakub Jelinek 2019-09-09 12:31:02 +02:00 • committed by Jakub Jelinek
parent b245befcdd
commit ca47c3987c
4 changed files with 28 additions and 1 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

4
gcc/ChangeLog
View file

@ -1,5 +1,9 @@
2019-09-09 Jakub Jelinek <jakub@redhat.com>
PR target/87853
* config/i386/emmintrin.h (_mm_cmpeq_epi8): Use casts to __v16qi
instead of __v16qs.
PR target/91704
* config/i386/avxintrin.h (__v32qs): New typedef.
* config/i386/avx2intrin.h (_mm256_cmpgt_epi8): Use casts to __v32qs

2
gcc/config/i386/emmintrin.h
View file

@ -1308,7 +1308,7 @@ _mm_xor_si128 (__m128i __A, __m128i __B)
extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_cmpeq_epi8 (__m128i __A, __m128i __B)
{
return (__m128i) ((__v16qs)__A == (__v16qs)__B);
return (__m128i) ((__v16qi)__A == (__v16qi)__B);
}
extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__))

3
gcc/testsuite/ChangeLog
View file

@ -1,5 +1,8 @@
2019-09-09 Jakub Jelinek <jakub@redhat.com>
PR target/87853
* gcc.target/i386/pr87853.c: New test.
PR target/91704
* gcc.target/i386/pr91704.c: New test.

20
gcc/testsuite/gcc.target/i386/pr87853.c Normal file
View file

@ -0,0 +1,20 @@
/* PR target/87853 */
/* { dg-do compile } */
/* { dg-options "-O2 -funsigned-char -msse2 -mno-sse3 -masm=att" } */
/* { dg-final { scan-assembler-times "\tpcmpgtb\t%xmm" 2 } } */
/* { dg-final { scan-assembler-not "\tpsubusb\t" } } */
/* { dg-final { scan-assembler-not "\tpcmpeqb\t" } } */
#include <x86intrin.h>
__m128i
foo (__m128i x, __m128i y)
{
return _mm_cmpgt_epi8 (x, y);
}
__m128i
bar (__m128i x, __m128i y)
{
return _mm_cmplt_epi8 (x, y);
}