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

	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: r275516

diff --git a/gcc/ChangeLog b/gcc/ChangeLog
index 94541446508c64851b4fef0de6cc97b7dd070157..18be6a493ce6dae9c9efd56894a8263abf72b3df 100644 (file)
--- a/gcc/ChangeLog
+++ b/gcc/ChangeLog
@@ -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

diff --git a/gcc/config/i386/emmintrin.h b/gcc/config/i386/emmintrin.h
index c35a20f710788ee624ea5e61fa622ddb6f8e3f9b..3c0104f6abdff9775e98eba7e8e9a912719b315f 100644 (file)
--- a/gcc/config/i386/emmintrin.h
+++ b/gcc/config/i386/emmintrin.h
@@ -1296,7 +1296,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__))

diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog
index d5064f48cca39ddc5f1959756cf0af53ef7161d3..24272ee404cb785ab76e72893248b4d2a73954d1 100644 (file)
--- a/gcc/testsuite/ChangeLog
+++ b/gcc/testsuite/ChangeLog
@@ -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.
 

diff --git a/gcc/testsuite/gcc.target/i386/pr87853.c b/gcc/testsuite/gcc.target/i386/pr87853.c
new file mode 100644 (file)
index 0000000..9a28887
--- /dev/null
+++ b/gcc/testsuite/gcc.target/i386/pr87853.c
@@ -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);
+}