432 lines · c
1// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror | FileCheck %s2// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror | FileCheck %s3// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror | FileCheck %s4// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror | FileCheck %s5// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror | FileCheck %s6// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror | FileCheck %s7// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror | FileCheck %s8// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror | FileCheck %s9 10// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s11// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s12// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s13// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s14// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s15// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s16// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s17// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +xop -fno-signed-char -emit-llvm -o - -Wall -Werror -fexperimental-new-constant-interpreter | FileCheck %s18 19 20#include <x86intrin.h>21#include "builtin_test_helpers.h"22 23// NOTE: This should match the tests in llvm/test/CodeGen/X86/xop-intrinsics-fast-isel.ll24 25__m128i test_mm_maccs_epi16(__m128i a, __m128i b, __m128i c) {26 // CHECK-LABEL: test_mm_maccs_epi1627 // CHECK: call <8 x i16> @llvm.x86.xop.vpmacssww(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}})28 return _mm_maccs_epi16(a, b, c);29}30 31__m128i test_mm_macc_epi16(__m128i a, __m128i b, __m128i c) {32 // CHECK-LABEL: test_mm_macc_epi1633 // CHECK: call <8 x i16> @llvm.x86.xop.vpmacsww(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}})34 return _mm_macc_epi16(a, b, c);35}36 37__m128i test_mm_maccsd_epi16(__m128i a, __m128i b, __m128i c) {38 // CHECK-LABEL: test_mm_maccsd_epi1639 // CHECK: call <4 x i32> @llvm.x86.xop.vpmacsswd(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <4 x i32> %{{.*}})40 return _mm_maccsd_epi16(a, b, c);41}42 43__m128i test_mm_maccd_epi16(__m128i a, __m128i b, __m128i c) {44 // CHECK-LABEL: test_mm_maccd_epi1645 // CHECK: call <4 x i32> @llvm.x86.xop.vpmacswd(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <4 x i32> %{{.*}})46 return _mm_maccd_epi16(a, b, c);47}48 49__m128i test_mm_maccs_epi32(__m128i a, __m128i b, __m128i c) {50 // CHECK-LABEL: test_mm_maccs_epi3251 // CHECK: call <4 x i32> @llvm.x86.xop.vpmacssdd(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})52 return _mm_maccs_epi32(a, b, c);53}54 55__m128i test_mm_macc_epi32(__m128i a, __m128i b, __m128i c) {56 // CHECK-LABEL: test_mm_macc_epi3257 // CHECK: call <4 x i32> @llvm.x86.xop.vpmacsdd(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})58 return _mm_macc_epi32(a, b, c);59}60 61__m128i test_mm_maccslo_epi32(__m128i a, __m128i b, __m128i c) {62 // CHECK-LABEL: test_mm_maccslo_epi3263 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vpmacssdql(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <2 x i64> %{{.*}})64 return _mm_maccslo_epi32(a, b, c);65}66 67__m128i test_mm_macclo_epi32(__m128i a, __m128i b, __m128i c) {68 // CHECK-LABEL: test_mm_macclo_epi3269 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vpmacsdql(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <2 x i64> %{{.*}})70 return _mm_macclo_epi32(a, b, c);71}72 73__m128i test_mm_maccshi_epi32(__m128i a, __m128i b, __m128i c) {74 // CHECK-LABEL: test_mm_maccshi_epi3275 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vpmacssdqh(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <2 x i64> %{{.*}})76 return _mm_maccshi_epi32(a, b, c);77}78 79__m128i test_mm_macchi_epi32(__m128i a, __m128i b, __m128i c) {80 // CHECK-LABEL: test_mm_macchi_epi3281 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vpmacsdqh(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <2 x i64> %{{.*}})82 return _mm_macchi_epi32(a, b, c);83}84 85__m128i test_mm_maddsd_epi16(__m128i a, __m128i b, __m128i c) {86 // CHECK-LABEL: test_mm_maddsd_epi1687 // CHECK: call <4 x i32> @llvm.x86.xop.vpmadcsswd(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <4 x i32> %{{.*}})88 return _mm_maddsd_epi16(a, b, c);89}90 91__m128i test_mm_maddd_epi16(__m128i a, __m128i b, __m128i c) {92 // CHECK-LABEL: test_mm_maddd_epi1693 // CHECK: call <4 x i32> @llvm.x86.xop.vpmadcswd(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <4 x i32> %{{.*}})94 return _mm_maddd_epi16(a, b, c);95}96 97__m128i test_mm_haddw_epi8(__m128i a) {98 // CHECK-LABEL: test_mm_haddw_epi899 // CHECK: call <8 x i16> @llvm.x86.xop.vphaddbw(<16 x i8> %{{.*}})100 return _mm_haddw_epi8(a);101}102 103__m128i test_mm_haddd_epi8(__m128i a) {104 // CHECK-LABEL: test_mm_haddd_epi8105 // CHECK: call <4 x i32> @llvm.x86.xop.vphaddbd(<16 x i8> %{{.*}})106 return _mm_haddd_epi8(a);107}108 109__m128i test_mm_haddq_epi8(__m128i a) {110 // CHECK-LABEL: test_mm_haddq_epi8111 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vphaddbq(<16 x i8> %{{.*}})112 return _mm_haddq_epi8(a);113}114 115__m128i test_mm_haddd_epi16(__m128i a) {116 // CHECK-LABEL: test_mm_haddd_epi16117 // CHECK: call <4 x i32> @llvm.x86.xop.vphaddwd(<8 x i16> %{{.*}})118 return _mm_haddd_epi16(a);119}120 121__m128i test_mm_haddq_epi16(__m128i a) {122 // CHECK-LABEL: test_mm_haddq_epi16123 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vphaddwq(<8 x i16> %{{.*}})124 return _mm_haddq_epi16(a);125}126 127__m128i test_mm_haddq_epi32(__m128i a) {128 // CHECK-LABEL: test_mm_haddq_epi32129 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vphadddq(<4 x i32> %{{.*}})130 return _mm_haddq_epi32(a);131}132 133__m128i test_mm_haddw_epu8(__m128i a) {134 // CHECK-LABEL: test_mm_haddw_epu8135 // CHECK: call <8 x i16> @llvm.x86.xop.vphaddubw(<16 x i8> %{{.*}})136 return _mm_haddw_epu8(a);137}138 139__m128i test_mm_haddd_epu8(__m128i a) {140 // CHECK-LABEL: test_mm_haddd_epu8141 // CHECK: call <4 x i32> @llvm.x86.xop.vphaddubd(<16 x i8> %{{.*}})142 return _mm_haddd_epu8(a);143}144 145__m128i test_mm_haddq_epu8(__m128i a) {146 // CHECK-LABEL: test_mm_haddq_epu8147 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vphaddubq(<16 x i8> %{{.*}})148 return _mm_haddq_epu8(a);149}150 151__m128i test_mm_haddd_epu16(__m128i a) {152 // CHECK-LABEL: test_mm_haddd_epu16153 // CHECK: call <4 x i32> @llvm.x86.xop.vphadduwd(<8 x i16> %{{.*}})154 return _mm_haddd_epu16(a);155}156 157__m128i test_mm_haddq_epu16(__m128i a) {158 // CHECK-LABEL: test_mm_haddq_epu16159 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vphadduwq(<8 x i16> %{{.*}})160 return _mm_haddq_epu16(a);161}162 163__m128i test_mm_haddq_epu32(__m128i a) {164 // CHECK-LABEL: test_mm_haddq_epu32165 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vphaddudq(<4 x i32> %{{.*}})166 return _mm_haddq_epu32(a);167}168 169__m128i test_mm_hsubw_epi8(__m128i a) {170 // CHECK-LABEL: test_mm_hsubw_epi8171 // CHECK: call <8 x i16> @llvm.x86.xop.vphsubbw(<16 x i8> %{{.*}})172 return _mm_hsubw_epi8(a);173}174 175__m128i test_mm_hsubd_epi16(__m128i a) {176 // CHECK-LABEL: test_mm_hsubd_epi16177 // CHECK: call <4 x i32> @llvm.x86.xop.vphsubwd(<8 x i16> %{{.*}})178 return _mm_hsubd_epi16(a);179}180 181__m128i test_mm_hsubq_epi32(__m128i a) {182 // CHECK-LABEL: test_mm_hsubq_epi32183 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vphsubdq(<4 x i32> %{{.*}})184 return _mm_hsubq_epi32(a);185}186 187__m128i test_mm_cmov_si128(__m128i a, __m128i b, __m128i c) {188 // CHECK-LABEL: test_mm_cmov_si128189 // CHECK: [[AND:%.*]] = and <2 x i64> %{{.*}}, %{{.*}}190 // CHECK: [[NEG:%.*]] = xor <2 x i64> %{{.*}}, splat (i64 -1)191 // CHECK-NEXT: [[ANDN:%.*]] = and <2 x i64> %{{.*}}, [[NEG]]192 // CHECK-NEXT: %{{.*}} = or <2 x i64> [[AND]], [[ANDN]]193 return _mm_cmov_si128(a, b, c);194}195TEST_CONSTEXPR(match_v4si(_mm_cmov_si128((__m128i)(__v4si){+1,+2,+3,+4}, (__m128i)(__v4si){-4,-3,-2,-1}, (__m128i)(__v4si){-1,0,0,-1}), +1, -3, -2, +4));196 197__m256i test_mm256_cmov_si256(__m256i a, __m256i b, __m256i c) {198 // CHECK-LABEL: test_mm256_cmov_si256199 // CHECK: [[AND:%.*]] = and <4 x i64> %{{.*}}, %{{.*}}200 // CHECK: [[NEG:%.*]] = xor <4 x i64> %{{.*}}, splat (i64 -1)201 // CHECK-NEXT: [[ANDN:%.*]] = and <4 x i64> %{{.*}}, [[NEG]]202 // CHECK-NEXT: %{{.*}} = or <4 x i64> [[AND]], [[ANDN]]203 return _mm256_cmov_si256(a, b, c);204}205TEST_CONSTEXPR(match_v4di(_mm256_cmov_si256((__m256i)(__v4di){+1,+2,+3,+4}, (__m256i)(__v4di){-4,-3,-2,-1}, (__m256i)(__v4di){0,-1,0,-1}), -4, +2, -2, +4));206 207__m128i test_mm_perm_epi8(__m128i a, __m128i b, __m128i c) {208 // CHECK-LABEL: test_mm_perm_epi8209 // CHECK: call <16 x i8> @llvm.x86.xop.vpperm(<16 x i8> %{{.*}}, <16 x i8> %{{.*}}, <16 x i8> %{{.*}})210 return _mm_perm_epi8(a, b, c);211}212 213__m128i test_mm_rot_epi8(__m128i a, __m128i b) {214 // CHECK-LABEL: test_mm_rot_epi8215 // CHECK: call <16 x i8> @llvm.fshl.v16i8(<16 x i8> %{{.*}}, <16 x i8> %{{.*}}, <16 x i8> %{{.*}})216 return _mm_rot_epi8(a, b);217}218TEST_CONSTEXPR(match_v16qi(_mm_rot_epi8((__m128i)(__v16qs){15, -14, -13, -12, 11, 10, 9, 8, 7, 6, 5, -4, 3, -2, 1, 0}, (__m128i)(__v16qs){0, 1, -2, 3, -4, 5, -6, 7, -8, 9, -10, 11, -12, 13, -14, 15}), 15, -27, -4, -89, -80, 65, 36, 4, 7, 12, 65, -25, 48, -33, 4, 0));219 220__m128i test_mm_rot_epi16(__m128i a, __m128i b) {221 // CHECK-LABEL: test_mm_rot_epi16222 // CHECK: call <8 x i16> @llvm.fshl.v8i16(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}})223 return _mm_rot_epi16(a, b);224}225TEST_CONSTEXPR(match_v8hi(_mm_rot_epi16((__m128i)(__v8hi){7, 6, 5, -4, 3, -2, 1, 0}, (__m128i)(__v8hi){0, 1, -2, 3, -4, 5, -6, 7}), 7, 12, 16385, -25, 12288, -33, 1024, 0));226 227__m128i test_mm_rot_epi32(__m128i a, __m128i b) {228 // CHECK-LABEL: test_mm_rot_epi32229 // CHECK: call <4 x i32> @llvm.fshl.v4i32(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})230 return _mm_rot_epi32(a, b);231}232TEST_CONSTEXPR(match_v4si(_mm_rot_epi32((__m128i)(__v4si){3, -2, 1, 0}, (__m128i)(__v4si){0, 1, -2, 3}), 3, -3, 1073741824, 0));233 234__m128i test_mm_rot_epi64(__m128i a, __m128i b) {235 // CHECK-LABEL: test_mm_rot_epi64236 // CHECK: call {{.*}}<2 x i64> @llvm.fshl.v2i64(<2 x i64> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}})237 return _mm_rot_epi64(a, b);238}239TEST_CONSTEXPR(match_v2di(_mm_rot_epi64((__m128i)(__v2di){99, -55}, (__m128i)(__v2di){1, -2}), 198, 9223372036854775794LL));240 241__m128i test_mm_roti_epi8(__m128i a) {242 // CHECK-LABEL: test_mm_roti_epi8243 // CHECK: call <16 x i8> @llvm.fshl.v16i8(<16 x i8> %{{.*}}, <16 x i8> %{{.*}}, <16 x i8> splat (i8 1))244 return _mm_roti_epi8(a, 1);245}246TEST_CONSTEXPR(match_v16qi(_mm_roti_epi8(((__m128i)(__v16qs){0, 1, -2, 3, -4, 5, -6, 7, -8, 9, -10, 11, -12, 13, -14, 15}), 3), 0, 8, -9, 24, -25, 40, -41, 56, -57, 72, -73, 88, -89, 104, -105, 120));247 248__m128i test_mm_roti_epi16(__m128i a) {249 // CHECK-LABEL: test_mm_roti_epi16250 // CHECK: call <8 x i16> @llvm.fshl.v8i16(<8 x i16> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> splat (i16 50))251 return _mm_roti_epi16(a, 50);252}253TEST_CONSTEXPR(match_v8hi(_mm_roti_epi16(((__m128i)(__v8hi){2, -3, 4, -5, 6, -7, 8, -9}), 1), 4, -5, 8, -9, 12, -13, 16, -17));254 255__m128i test_mm_roti_epi32(__m128i a) {256 // CHECK-LABEL: test_mm_roti_epi32257 // CHECK: call <4 x i32> @llvm.fshl.v4i32(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> splat (i32 226))258 return _mm_roti_epi32(a, -30);259}260TEST_CONSTEXPR(match_v4si(_mm_roti_epi32(((__m128i)(__v4si){1, -2, 3, -4}), 5), 32, -33, 96, -97));261 262__m128i test_mm_roti_epi64(__m128i a) {263 // CHECK-LABEL: test_mm_roti_epi64264 // CHECK: call {{.*}}<2 x i64> @llvm.fshl.v2i64(<2 x i64> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> splat (i64 100))265 return _mm_roti_epi64(a, 100);266}267TEST_CONSTEXPR(match_v2di(_mm_roti_epi64(((__m128i)(__v2di){99, -55}), 19), 51904512, -28311553));268 269__m128i test_mm_shl_epi8(__m128i a, __m128i b) {270 // CHECK-LABEL: test_mm_shl_epi8271 // CHECK: call <16 x i8> @llvm.x86.xop.vpshlb(<16 x i8> %{{.*}}, <16 x i8> %{{.*}})272 return _mm_shl_epi8(a, b);273}274 275__m128i test_mm_shl_epi16(__m128i a, __m128i b) {276 // CHECK-LABEL: test_mm_shl_epi16277 // CHECK: call <8 x i16> @llvm.x86.xop.vpshlw(<8 x i16> %{{.*}}, <8 x i16> %{{.*}})278 return _mm_shl_epi16(a, b);279}280 281__m128i test_mm_shl_epi32(__m128i a, __m128i b) {282 // CHECK-LABEL: test_mm_shl_epi32283 // CHECK: call <4 x i32> @llvm.x86.xop.vpshld(<4 x i32> %{{.*}}, <4 x i32> %{{.*}})284 return _mm_shl_epi32(a, b);285}286 287__m128i test_mm_shl_epi64(__m128i a, __m128i b) {288 // CHECK-LABEL: test_mm_shl_epi64289 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vpshlq(<2 x i64> %{{.*}}, <2 x i64> %{{.*}})290 return _mm_shl_epi64(a, b);291}292 293__m128i test_mm_sha_epi8(__m128i a, __m128i b) {294 // CHECK-LABEL: test_mm_sha_epi8295 // CHECK: call <16 x i8> @llvm.x86.xop.vpshab(<16 x i8> %{{.*}}, <16 x i8> %{{.*}})296 return _mm_sha_epi8(a, b);297}298 299__m128i test_mm_sha_epi16(__m128i a, __m128i b) {300 // CHECK-LABEL: test_mm_sha_epi16301 // CHECK: call <8 x i16> @llvm.x86.xop.vpshaw(<8 x i16> %{{.*}}, <8 x i16> %{{.*}})302 return _mm_sha_epi16(a, b);303}304 305__m128i test_mm_sha_epi32(__m128i a, __m128i b) {306 // CHECK-LABEL: test_mm_sha_epi32307 // CHECK: call <4 x i32> @llvm.x86.xop.vpshad(<4 x i32> %{{.*}}, <4 x i32> %{{.*}})308 return _mm_sha_epi32(a, b);309}310 311__m128i test_mm_sha_epi64(__m128i a, __m128i b) {312 // CHECK-LABEL: test_mm_sha_epi64313 // CHECK: call {{.*}}<2 x i64> @llvm.x86.xop.vpshaq(<2 x i64> %{{.*}}, <2 x i64> %{{.*}})314 return _mm_sha_epi64(a, b);315}316 317__m128i test_mm_com_epu8(__m128i a, __m128i b) {318 // CHECK-LABEL: test_mm_com_epu8319 // CHECK: icmp ult <16 x i8> %{{.*}}, %{{.*}}320 // CHECK: sext <16 x i1> %{{.*}} to <16 x i8>321 return _mm_com_epu8(a, b, 0);322}323 324__m128i test_mm_com_epu16(__m128i a, __m128i b) {325 // CHECK-LABEL: test_mm_com_epu16326 // CHECK: icmp ult <8 x i16> %{{.*}}, %{{.*}}327 // CHECK: sext <8 x i1> %{{.*}} to <8 x i16>328 return _mm_com_epu16(a, b, 0);329}330 331__m128i test_mm_com_epu32(__m128i a, __m128i b) {332 // CHECK-LABEL: test_mm_com_epu32333 // CHECK: icmp ult <4 x i32> %{{.*}}, %{{.*}}334 // CHECK: sext <4 x i1> %{{.*}} to <4 x i32>335 return _mm_com_epu32(a, b, 0);336}337 338__m128i test_mm_com_epu64(__m128i a, __m128i b) {339 // CHECK-LABEL: test_mm_com_epu64340 // CHECK: icmp ult <2 x i64> %{{.*}}, %{{.*}}341 // CHECK: sext <2 x i1> %{{.*}} to <2 x i64>342 return _mm_com_epu64(a, b, 0);343}344 345__m128i test_mm_com_epi8(__m128i a, __m128i b) {346 // CHECK-LABEL: test_mm_com_epi8347 // CHECK: icmp slt <16 x i8> %{{.*}}, %{{.*}}348 // CHECK: sext <16 x i1> %{{.*}} to <16 x i8>349 return _mm_com_epi8(a, b, 0);350}351 352__m128i test_mm_com_epi16(__m128i a, __m128i b) {353 // CHECK-LABEL: test_mm_com_epi16354 // CHECK: icmp slt <8 x i16> %{{.*}}, %{{.*}}355 // CHECK: sext <8 x i1> %{{.*}} to <8 x i16>356 return _mm_com_epi16(a, b, 0);357}358 359__m128i test_mm_com_epi32(__m128i a, __m128i b) {360 // CHECK-LABEL: test_mm_com_epi32361 // CHECK: icmp slt <4 x i32> %{{.*}}, %{{.*}}362 // CHECK: sext <4 x i1> %{{.*}} to <4 x i32>363 return _mm_com_epi32(a, b, 0);364}365 366__m128i test_mm_com_epi64(__m128i a, __m128i b) {367 // CHECK-LABEL: test_mm_com_epi64368 // CHECK: icmp slt <2 x i64> %{{.*}}, %{{.*}}369 // CHECK: sext <2 x i1> %{{.*}} to <2 x i64>370 return _mm_com_epi64(a, b, 0);371}372 373__m128d test_mm_permute2_pd(__m128d a, __m128d b, __m128i c) {374 // CHECK-LABEL: test_mm_permute2_pd375 // CHECK: call <2 x double> @llvm.x86.xop.vpermil2pd(<2 x double> %{{.*}}, <2 x double> %{{.*}}, <2 x i64> %{{.*}}, i8 0)376 return _mm_permute2_pd(a, b, c, 0);377}378 379__m256d test_mm256_permute2_pd(__m256d a, __m256d b, __m256i c) {380 // CHECK-LABEL: test_mm256_permute2_pd381 // CHECK: call <4 x double> @llvm.x86.xop.vpermil2pd.256(<4 x double> %{{.*}}, <4 x double> %{{.*}}, <4 x i64> %{{.*}}, i8 0)382 return _mm256_permute2_pd(a, b, c, 0);383}384 385__m128 test_mm_permute2_ps(__m128 a, __m128 b, __m128i c) {386 // CHECK-LABEL: test_mm_permute2_ps387 // CHECK: call <4 x float> @llvm.x86.xop.vpermil2ps(<4 x float> %{{.*}}, <4 x float> %{{.*}}, <4 x i32> %{{.*}}, i8 0)388 return _mm_permute2_ps(a, b, c, 0);389}390 391__m256 test_mm256_permute2_ps(__m256 a, __m256 b, __m256i c) {392 // CHECK-LABEL: test_mm256_permute2_ps393 // CHECK: call <8 x float> @llvm.x86.xop.vpermil2ps.256(<8 x float> %{{.*}}, <8 x float> %{{.*}}, <8 x i32> %{{.*}}, i8 0)394 return _mm256_permute2_ps(a, b, c, 0);395}396 397__m128 test_mm_frcz_ss(__m128 a) {398 // CHECK-LABEL: test_mm_frcz_ss399 // CHECK: call {{.*}}<4 x float> @llvm.x86.xop.vfrcz.ss(<4 x float> %{{.*}})400 return _mm_frcz_ss(a);401}402 403__m128d test_mm_frcz_sd(__m128d a) {404 // CHECK-LABEL: test_mm_frcz_sd405 // CHECK: call {{.*}}<2 x double> @llvm.x86.xop.vfrcz.sd(<2 x double> %{{.*}})406 return _mm_frcz_sd(a);407}408 409__m128 test_mm_frcz_ps(__m128 a) {410 // CHECK-LABEL: test_mm_frcz_ps411 // CHECK: call {{.*}}<4 x float> @llvm.x86.xop.vfrcz.ps(<4 x float> %{{.*}})412 return _mm_frcz_ps(a);413}414 415__m128d test_mm_frcz_pd(__m128d a) {416 // CHECK-LABEL: test_mm_frcz_pd417 // CHECK: call {{.*}}<2 x double> @llvm.x86.xop.vfrcz.pd(<2 x double> %{{.*}})418 return _mm_frcz_pd(a);419}420 421__m256 test_mm256_frcz_ps(__m256 a) {422 // CHECK-LABEL: test_mm256_frcz_ps423 // CHECK: call {{.*}}<8 x float> @llvm.x86.xop.vfrcz.ps.256(<8 x float> %{{.*}})424 return _mm256_frcz_ps(a);425}426 427__m256d test_mm256_frcz_pd(__m256d a) {428 // CHECK-LABEL: test_mm256_frcz_pd429 // CHECK: call {{.*}}<4 x double> @llvm.x86.xop.vfrcz.pd.256(<4 x double> %{{.*}})430 return _mm256_frcz_pd(a);431}432