diff --git a/lib/Headers/avxintrin.h b/lib/Headers/avxintrin.h index 20e9ef4e57600c86f620accb9a093a10e0bf382e..a71bd7a9934a17ef7f54ef37dca53d1d12204d8b 100644 --- a/lib/Headers/avxintrin.h +++ b/lib/Headers/avxintrin.h @@ -1875,13 +1875,13 @@ _mm256_extract_epi32(__m256i __a, const int __imm) /// \param __imm /// An immediate integer operand with bits [3:0] determining which vector /// element is extracted and returned. -/// \returns A 32-bit integer containing the extracted 16 bits of extended +/// \returns A 32-bit integer containing the extracted 16 bits of zero extended /// packed data. static __inline int __DEFAULT_FN_ATTRS _mm256_extract_epi16(__m256i __a, const int __imm) { __v16hi __b = (__v16hi)__a; - return __b[__imm & 15]; + return (unsigned short)__b[__imm & 15]; } /// \brief Takes a [32 x i8] vector and returns the vector element value @@ -1897,13 +1897,13 @@ _mm256_extract_epi16(__m256i __a, const int __imm) /// \param __imm /// An immediate integer operand with bits [4:0] determining which vector /// element is extracted and returned. -/// \returns A 32-bit integer containing the extracted 8 bits of extended packed -/// data. +/// \returns A 32-bit integer containing the extracted 8 bits of zero extended +/// packed data. static __inline int __DEFAULT_FN_ATTRS _mm256_extract_epi8(__m256i __a, const int __imm) { __v32qi __b = (__v32qi)__a; - return __b[__imm & 31]; + return (unsigned char)__b[__imm & 31]; } #ifdef __x86_64__ diff --git a/test/CodeGen/avx-builtins.c b/test/CodeGen/avx-builtins.c index 23bc65448080c3122f19d5ac742f998615d685f0..ad187e805caf9668b246ae11f8018f6132f44d32 100644 --- a/test/CodeGen/avx-builtins.c +++ b/test/CodeGen/avx-builtins.c @@ -314,21 +314,19 @@ __m256 test_mm256_dp_ps(__m256 A, __m256 B) { return _mm256_dp_ps(A, B, 7); } -// FIXME: ZEXT instead of SEXT int test_mm256_extract_epi8(__m256i A) { // CHECK-LABEL: test_mm256_extract_epi8 // CHECK: and i32 %{{.*}}, 31 // CHECK: extractelement <32 x i8> %{{.*}}, i32 %{{.*}} - // CHECK: ext i8 %{{.*}} to i32 + // CHECK: zext i8 %{{.*}} to i32 return _mm256_extract_epi8(A, 32); } -// FIXME: ZEXT instead of SEXT int test_mm256_extract_epi16(__m256i A) { // CHECK-LABEL: test_mm256_extract_epi16 // CHECK: and i32 %{{.*}}, 15 // CHECK: extractelement <16 x i16> %{{.*}}, i32 %{{.*}} - // CHECK: ext i16 %{{.*}} to i32 + // CHECK: zext i16 %{{.*}} to i32 return _mm256_extract_epi16(A, 16); }