This is an archive of the discontinued LLVM Phabricator instance.

Differential D80251

[X86] Update some av512 shift intrinsics to use "unsigned int" parameter instead of int to match Intel documentaiton
ClosedPublic

Authored by craig.topper on May 19 2020, 2:51 PM.

Details

Reviewers
RKSimon
spatel
Commits
rG1b02db52b79e: [X86] Update some av512 shift intrinsics to use "unsigned int" parameter…
Summary

There are 65 that take a scalar shift amount. Intel documentation shows 60 of them taking unsigned int. There are 5 versions of srli_epi16 that use int, the 512-bit maskz and 128/256 mask/maskz.

Fixes PR45931

Diff Detail

Event Timeline

craig.topper created this revision.May 19 2020, 2:51 PM
spatel added a comment.May 20 2020, 6:07 AM

Is it possible to fix those other 5 in the Intel docs for consistency, or is there some functional reason that those are different?

craig.topper added a comment.May 20 2020, 3:19 PM
In D80251#2046564, @spatel wrote:

Is it possible to fix those other 5 in the Intel docs for consistency, or is there some functional reason that those are different?

I think it was just a mistake. The docs are derived from icc's source code which also has them wrong. Note all of the SSE/AVX2 shift intrinsics use int not unsigned int.

RKSimon added a comment.May 21 2020, 10:19 AM

Can we add -Wsign-conversion checks to the tests? That was mentioned on PR45931

craig.topper added a comment.May 21 2020, 1:59 PM
In D80251#2049418, @RKSimon wrote:

Can we add -Wsign-conversion checks to the tests? That was mentioned on PR45931

I can. Will that do anything other than show that my test_* functions were updated to match the new type?

RKSimon accepted this revision.May 22 2020, 8:31 AM
In D80251#2049975, @craig.topper wrote:
In D80251#2049418, @RKSimon wrote:

Can we add -Wsign-conversion checks to the tests? That was mentioned on PR45931

I can. Will that do anything other than show that my test_* functions were updated to match the new type?

not much other than check for regressions again tbh.

otherwise, lgtm

This revision is now accepted and ready to land.May 22 2020, 8:31 AM
craig.topper updated this revision to Diff 265787.May 22 2020, 12:47 PM

Add -Wsign-conversion. Fix two test issues that exposed.

Closed by commit rG1b02db52b79e: [X86] Update some av512 shift intrinsics to use "unsigned int" parameter… (authored by craig.topper). · Explain WhyMay 22 2020, 9:25 PM
This revision was automatically updated to reflect the committed changes.
Herald added a project: Restricted Project. · View Herald TranscriptMay 22 2020, 9:25 PM

Revision Contents

PathSize
clang/
lib/
Headers/
19 lines
42 lines
18 lines
53 lines
test/
CodeGen/
20 lines
44 lines
58 lines
20 lines

Diff 265835

clang/lib/Headers/avx512bwintrin.h

Show First 20 Lines • Show All 1,498 Lines • ▼ Show 20 Lines
_mm512_maskz_sll_epi16(__mmask32 __U, __m512i __A, __m128i __B) _mm512_maskz_sll_epi16(__mmask32 __U, __m512i __A, __m128i __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_sll_epi16(__A, __B), (__v32hi)_mm512_sll_epi16(__A, __B),
(__v32hi)_mm512_setzero_si512()); (__v32hi)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_slli_epi16(__m512i __A, int __B) _mm512_slli_epi16(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psllwi512((__v32hi)__A, __B); return (__m512i)__builtin_ia32_psllwi512((__v32hi)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_slli_epi16(__m512i __W, __mmask32 __U, __m512i __A, int __B) _mm512_mask_slli_epi16(__m512i __W, __mmask32 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_slli_epi16(__A, __B), (__v32hi)_mm512_slli_epi16(__A, __B),
(__v32hi)__W); (__v32hi)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_slli_epi16(__mmask32 __U, __m512i __A, int __B) _mm512_maskz_slli_epi16(__mmask32 __U, __m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_slli_epi16(__A, __B), (__v32hi)_mm512_slli_epi16(__A, __B),
(__v32hi)_mm512_setzero_si512()); (__v32hi)_mm512_setzero_si512());
} }
#define _mm512_bslli_epi128(a, imm) \ #define _mm512_bslli_epi128(a, imm) \
(__m512i)__builtin_ia32_pslldqi512_byteshift((__v8di)(__m512i)(a), (int)(imm)) (__m512i)__builtin_ia32_pslldqi512_byteshift((__v8di)(__m512i)(a), (int)(imm))
▲ Show 20 Lines • Show All 60 Lines • ▼ Show 20 Lines
_mm512_maskz_sra_epi16(__mmask32 __U, __m512i __A, __m128i __B) _mm512_maskz_sra_epi16(__mmask32 __U, __m512i __A, __m128i __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_sra_epi16(__A, __B), (__v32hi)_mm512_sra_epi16(__A, __B),
(__v32hi)_mm512_setzero_si512()); (__v32hi)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_srai_epi16(__m512i __A, int __B) _mm512_srai_epi16(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psrawi512((__v32hi)__A, __B); return (__m512i)__builtin_ia32_psrawi512((__v32hi)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_srai_epi16(__m512i __W, __mmask32 __U, __m512i __A, int __B) _mm512_mask_srai_epi16(__m512i __W, __mmask32 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_srai_epi16(__A, __B), (__v32hi)_mm512_srai_epi16(__A, __B),
(__v32hi)__W); (__v32hi)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_srai_epi16(__mmask32 __U, __m512i __A, int __B) _mm512_maskz_srai_epi16(__mmask32 __U, __m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_srai_epi16(__A, __B), (__v32hi)_mm512_srai_epi16(__A, __B),
(__v32hi)_mm512_setzero_si512()); (__v32hi)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_srl_epi16(__m512i __A, __m128i __B) _mm512_srl_epi16(__m512i __A, __m128i __B)
Show All 13 Lines
_mm512_maskz_srl_epi16(__mmask32 __U, __m512i __A, __m128i __B) _mm512_maskz_srl_epi16(__mmask32 __U, __m512i __A, __m128i __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_srl_epi16(__A, __B), (__v32hi)_mm512_srl_epi16(__A, __B),
(__v32hi)_mm512_setzero_si512()); (__v32hi)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_srli_epi16(__m512i __A, int __B) _mm512_srli_epi16(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psrlwi512((__v32hi)__A, __B); return (__m512i)__builtin_ia32_psrlwi512((__v32hi)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_srli_epi16(__m512i __W, __mmask32 __U, __m512i __A, int __B) _mm512_mask_srli_epi16(__m512i __W, __mmask32 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U, return (__m512i)__builtin_ia32_selectw_512((__mmask32)__U,
(__v32hi)_mm512_srli_epi16(__A, __B), (__v32hi)_mm512_srli_epi16(__A, __B),
(__v32hi)__W); (__v32hi)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_srli_epi16(__mmask32 __U, __m512i __A, int __B) _mm512_maskz_srli_epi16(__mmask32 __U, __m512i __A, int __B)
▲ Show 20 Lines • Show All 365 Lines • Show Last 20 Lines

clang/lib/Headers/avx512fintrin.h

  • This file is larger than 256 KB, so syntax highlighting is disabled by default.
Show First 20 Lines • Show All 5,105 Lines • ▼ Show 20 Lines (__m512i)__builtin_ia32_selectq_512((__mmask8)(U), \
(__v8di)(__m512i)(W)) (__v8di)(__m512i)(W))
#define _mm512_maskz_ror_epi64(U, A, B) \ #define _mm512_maskz_ror_epi64(U, A, B) \
(__m512i)__builtin_ia32_selectq_512((__mmask8)(U), \ (__m512i)__builtin_ia32_selectq_512((__mmask8)(U), \
(__v8di)_mm512_ror_epi64((A), (B)), \ (__v8di)_mm512_ror_epi64((A), (B)), \
(__v8di)_mm512_setzero_si512()) (__v8di)_mm512_setzero_si512())
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_slli_epi32(__m512i __A, int __B) _mm512_slli_epi32(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_pslldi512((__v16si)__A, __B); return (__m512i)__builtin_ia32_pslldi512((__v16si)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_slli_epi32(__m512i __W, __mmask16 __U, __m512i __A, int __B) _mm512_mask_slli_epi32(__m512i __W, __mmask16 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U, return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U,
(__v16si)_mm512_slli_epi32(__A, __B), (__v16si)_mm512_slli_epi32(__A, __B),
(__v16si)__W); (__v16si)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_slli_epi32(__mmask16 __U, __m512i __A, int __B) { _mm512_maskz_slli_epi32(__mmask16 __U, __m512i __A, unsigned int __B) {
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U, return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U,
(__v16si)_mm512_slli_epi32(__A, __B), (__v16si)_mm512_slli_epi32(__A, __B),
(__v16si)_mm512_setzero_si512()); (__v16si)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_slli_epi64(__m512i __A, int __B) _mm512_slli_epi64(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psllqi512((__v8di)__A, __B); return (__m512i)__builtin_ia32_psllqi512((__v8di)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_slli_epi64(__m512i __W, __mmask8 __U, __m512i __A, int __B) _mm512_mask_slli_epi64(__m512i __W, __mmask8 __U, __m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U, return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,
(__v8di)_mm512_slli_epi64(__A, __B), (__v8di)_mm512_slli_epi64(__A, __B),
(__v8di)__W); (__v8di)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_slli_epi64(__mmask8 __U, __m512i __A, int __B) _mm512_maskz_slli_epi64(__mmask8 __U, __m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U, return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,
(__v8di)_mm512_slli_epi64(__A, __B), (__v8di)_mm512_slli_epi64(__A, __B),
(__v8di)_mm512_setzero_si512()); (__v8di)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_srli_epi32(__m512i __A, int __B) _mm512_srli_epi32(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psrldi512((__v16si)__A, __B); return (__m512i)__builtin_ia32_psrldi512((__v16si)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_srli_epi32(__m512i __W, __mmask16 __U, __m512i __A, int __B) _mm512_mask_srli_epi32(__m512i __W, __mmask16 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U, return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U,
(__v16si)_mm512_srli_epi32(__A, __B), (__v16si)_mm512_srli_epi32(__A, __B),
(__v16si)__W); (__v16si)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_srli_epi32(__mmask16 __U, __m512i __A, int __B) { _mm512_maskz_srli_epi32(__mmask16 __U, __m512i __A, unsigned int __B) {
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U, return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U,
(__v16si)_mm512_srli_epi32(__A, __B), (__v16si)_mm512_srli_epi32(__A, __B),
(__v16si)_mm512_setzero_si512()); (__v16si)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_srli_epi64(__m512i __A, int __B) _mm512_srli_epi64(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psrlqi512((__v8di)__A, __B); return (__m512i)__builtin_ia32_psrlqi512((__v8di)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_srli_epi64(__m512i __W, __mmask8 __U, __m512i __A, int __B) _mm512_mask_srli_epi64(__m512i __W, __mmask8 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U, return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,
(__v8di)_mm512_srli_epi64(__A, __B), (__v8di)_mm512_srli_epi64(__A, __B),
(__v8di)__W); (__v8di)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_srli_epi64(__mmask8 __U, __m512i __A, int __B) _mm512_maskz_srli_epi64(__mmask8 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U, return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,
(__v8di)_mm512_srli_epi64(__A, __B), (__v8di)_mm512_srli_epi64(__A, __B),
(__v8di)_mm512_setzero_si512()); (__v8di)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_load_epi32 (__m512i __W, __mmask16 __U, void const *__P) _mm512_mask_load_epi32 (__m512i __W, __mmask16 __U, void const *__P)
▲ Show 20 Lines • Show All 1,387 Lines • ▼ Show 20 Lines
#define _mm_maskz_scalef_round_ss(U, A, B, R) \ #define _mm_maskz_scalef_round_ss(U, A, B, R) \
(__m128)__builtin_ia32_scalefss_round_mask((__v4sf)(__m128)(A), \ (__m128)__builtin_ia32_scalefss_round_mask((__v4sf)(__m128)(A), \
(__v4sf)(__m128)(B), \ (__v4sf)(__m128)(B), \
(__v4sf)_mm_setzero_ps(), \ (__v4sf)_mm_setzero_ps(), \
(__mmask8)(U), \ (__mmask8)(U), \
(int)(R)) (int)(R))
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_srai_epi32(__m512i __A, int __B) _mm512_srai_epi32(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psradi512((__v16si)__A, __B); return (__m512i)__builtin_ia32_psradi512((__v16si)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_srai_epi32(__m512i __W, __mmask16 __U, __m512i __A, int __B) _mm512_mask_srai_epi32(__m512i __W, __mmask16 __U, __m512i __A,
unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U, return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U,
(__v16si)_mm512_srai_epi32(__A, __B), (__v16si)_mm512_srai_epi32(__A, __B),
(__v16si)__W); (__v16si)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_srai_epi32(__mmask16 __U, __m512i __A, int __B) { _mm512_maskz_srai_epi32(__mmask16 __U, __m512i __A,
unsigned int __B) {
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U, return (__m512i)__builtin_ia32_selectd_512((__mmask16)__U,
(__v16si)_mm512_srai_epi32(__A, __B), (__v16si)_mm512_srai_epi32(__A, __B),
(__v16si)_mm512_setzero_si512()); (__v16si)_mm512_setzero_si512());
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_srai_epi64(__m512i __A, int __B) _mm512_srai_epi64(__m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_psraqi512((__v8di)__A, __B); return (__m512i)__builtin_ia32_psraqi512((__v8di)__A, __B);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_mask_srai_epi64(__m512i __W, __mmask8 __U, __m512i __A, int __B) _mm512_mask_srai_epi64(__m512i __W, __mmask8 __U, __m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U, return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,
(__v8di)_mm512_srai_epi64(__A, __B), (__v8di)_mm512_srai_epi64(__A, __B),
(__v8di)__W); (__v8di)__W);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS512 static __inline__ __m512i __DEFAULT_FN_ATTRS512
_mm512_maskz_srai_epi64(__mmask8 __U, __m512i __A, int __B) _mm512_maskz_srai_epi64(__mmask8 __U, __m512i __A, unsigned int __B)
{ {
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U, return (__m512i)__builtin_ia32_selectq_512((__mmask8)__U,
(__v8di)_mm512_srai_epi64(__A, __B), (__v8di)_mm512_srai_epi64(__A, __B),
(__v8di)_mm512_setzero_si512()); (__v8di)_mm512_setzero_si512());
} }
#define _mm512_shuffle_f32x4(A, B, imm) \ #define _mm512_shuffle_f32x4(A, B, imm) \
(__m512)__builtin_ia32_shuf_f32x4((__v16sf)(__m512)(A), \ (__m512)__builtin_ia32_shuf_f32x4((__v16sf)(__m512)(A), \
▲ Show 20 Lines • Show All 3,044 Lines • Show Last 20 Lines

clang/lib/Headers/avx512vlbwintrin.h

Show First 20 Lines • Show All 1,933 Lines • ▼ Show 20 Lines
_mm256_maskz_sll_epi16(__mmask16 __U, __m256i __A, __m128i __B) _mm256_maskz_sll_epi16(__mmask16 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U, return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U,
(__v16hi)_mm256_sll_epi16(__A, __B), (__v16hi)_mm256_sll_epi16(__A, __B),
(__v16hi)_mm256_setzero_si256()); (__v16hi)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_slli_epi16(__m128i __W, __mmask8 __U, __m128i __A, int __B) _mm_mask_slli_epi16(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U,
(__v8hi)_mm_slli_epi16(__A, __B), (__v8hi)_mm_slli_epi16(__A, __B),
(__v8hi)__W); (__v8hi)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_slli_epi16 (__mmask8 __U, __m128i __A, int __B) _mm_maskz_slli_epi16 (__mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U,
(__v8hi)_mm_slli_epi16(__A, __B), (__v8hi)_mm_slli_epi16(__A, __B),
(__v8hi)_mm_setzero_si128()); (__v8hi)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_slli_epi16(__m256i __W, __mmask16 __U, __m256i __A, int __B) _mm256_mask_slli_epi16(__m256i __W, __mmask16 __U, __m256i __A,
unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U, return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U,
(__v16hi)_mm256_slli_epi16(__A, __B), (__v16hi)_mm256_slli_epi16(__A, __B),
(__v16hi)__W); (__v16hi)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_slli_epi16(__mmask16 __U, __m256i __A, int __B) _mm256_maskz_slli_epi16(__mmask16 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U, return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U,
(__v16hi)_mm256_slli_epi16(__A, __B), (__v16hi)_mm256_slli_epi16(__A, __B),
(__v16hi)_mm256_setzero_si256()); (__v16hi)_mm256_setzero_si256());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_srlv_epi16(__m256i __A, __m256i __B) _mm256_srlv_epi16(__m256i __A, __m256i __B)
▲ Show 20 Lines • Show All 111 Lines • ▼ Show 20 Lines
_mm256_maskz_sra_epi16(__mmask16 __U, __m256i __A, __m128i __B) _mm256_maskz_sra_epi16(__mmask16 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U, return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U,
(__v16hi)_mm256_sra_epi16(__A, __B), (__v16hi)_mm256_sra_epi16(__A, __B),
(__v16hi)_mm256_setzero_si256()); (__v16hi)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srai_epi16(__m128i __W, __mmask8 __U, __m128i __A, int __B) _mm_mask_srai_epi16(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U,
(__v8hi)_mm_srai_epi16(__A, __B), (__v8hi)_mm_srai_epi16(__A, __B),
(__v8hi)__W); (__v8hi)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_srai_epi16(__mmask8 __U, __m128i __A, int __B) _mm_maskz_srai_epi16(__mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectw_128((__mmask8)__U,
(__v8hi)_mm_srai_epi16(__A, __B), (__v8hi)_mm_srai_epi16(__A, __B),
(__v8hi)_mm_setzero_si128()); (__v8hi)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_srai_epi16(__m256i __W, __mmask16 __U, __m256i __A, int __B) _mm256_mask_srai_epi16(__m256i __W, __mmask16 __U, __m256i __A,
unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U, return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U,
(__v16hi)_mm256_srai_epi16(__A, __B), (__v16hi)_mm256_srai_epi16(__A, __B),
(__v16hi)__W); (__v16hi)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_srai_epi16(__mmask16 __U, __m256i __A, int __B) _mm256_maskz_srai_epi16(__mmask16 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U, return (__m256i)__builtin_ia32_selectw_256((__mmask16)__U,
(__v16hi)_mm256_srai_epi16(__A, __B), (__v16hi)_mm256_srai_epi16(__A, __B),
(__v16hi)_mm256_setzero_si256()); (__v16hi)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srl_epi16(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) _mm_mask_srl_epi16(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B)
▲ Show 20 Lines • Show All 681 Lines • Show Last 20 Lines

clang/lib/Headers/avx512vlintrin.h

  • This file is larger than 256 KB, so syntax highlighting is disabled by default.
Show First 20 Lines • Show All 4,516 Lines • ▼ Show 20 Lines
_mm256_maskz_sll_epi32(__mmask8 __U, __m256i __A, __m128i __B) _mm256_maskz_sll_epi32(__mmask8 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_sll_epi32(__A, __B), (__v8si)_mm256_sll_epi32(__A, __B),
(__v8si)_mm256_setzero_si256()); (__v8si)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_slli_epi32(__m128i __W, __mmask8 __U, __m128i __A, int __B) _mm_mask_slli_epi32(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U,
(__v4si)_mm_slli_epi32(__A, __B), (__v4si)_mm_slli_epi32(__A, __B),
(__v4si)__W); (__v4si)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_slli_epi32(__mmask8 __U, __m128i __A, int __B) _mm_maskz_slli_epi32(__mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U,
(__v4si)_mm_slli_epi32(__A, __B), (__v4si)_mm_slli_epi32(__A, __B),
(__v4si)_mm_setzero_si128()); (__v4si)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_slli_epi32(__m256i __W, __mmask8 __U, __m256i __A, int __B) _mm256_mask_slli_epi32(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_slli_epi32(__A, __B), (__v8si)_mm256_slli_epi32(__A, __B),
(__v8si)__W); (__v8si)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_slli_epi32(__mmask8 __U, __m256i __A, int __B) _mm256_maskz_slli_epi32(__mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_slli_epi32(__A, __B), (__v8si)_mm256_slli_epi32(__A, __B),
(__v8si)_mm256_setzero_si256()); (__v8si)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_sll_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) _mm_mask_sll_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B)
Show All 23 Lines
_mm256_maskz_sll_epi64(__mmask8 __U, __m256i __A, __m128i __B) _mm256_maskz_sll_epi64(__mmask8 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U,
(__v4di)_mm256_sll_epi64(__A, __B), (__v4di)_mm256_sll_epi64(__A, __B),
(__v4di)_mm256_setzero_si256()); (__v4di)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_slli_epi64(__m128i __W, __mmask8 __U, __m128i __A, int __B) _mm_mask_slli_epi64(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U,
(__v2di)_mm_slli_epi64(__A, __B), (__v2di)_mm_slli_epi64(__A, __B),
(__v2di)__W); (__v2di)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_slli_epi64(__mmask8 __U, __m128i __A, int __B) _mm_maskz_slli_epi64(__mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U,
(__v2di)_mm_slli_epi64(__A, __B), (__v2di)_mm_slli_epi64(__A, __B),
(__v2di)_mm_setzero_si128()); (__v2di)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_slli_epi64(__m256i __W, __mmask8 __U, __m256i __A, int __B) _mm256_mask_slli_epi64(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U,
(__v4di)_mm256_slli_epi64(__A, __B), (__v4di)_mm256_slli_epi64(__A, __B),
(__v4di)__W); (__v4di)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_slli_epi64(__mmask8 __U, __m256i __A, int __B) _mm256_maskz_slli_epi64(__mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U,
(__v4di)_mm256_slli_epi64(__A, __B), (__v4di)_mm256_slli_epi64(__A, __B),
(__v4di)_mm256_setzero_si256()); (__v4di)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_rorv_epi32 (__m128i __A, __m128i __B) _mm_rorv_epi32 (__m128i __A, __m128i __B)
▲ Show 20 Lines • Show All 239 Lines • ▼ Show 20 Lines
_mm256_maskz_srl_epi32(__mmask8 __U, __m256i __A, __m128i __B) _mm256_maskz_srl_epi32(__mmask8 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_srl_epi32(__A, __B), (__v8si)_mm256_srl_epi32(__A, __B),
(__v8si)_mm256_setzero_si256()); (__v8si)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srli_epi32(__m128i __W, __mmask8 __U, __m128i __A, int __B) _mm_mask_srli_epi32(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U,
(__v4si)_mm_srli_epi32(__A, __B), (__v4si)_mm_srli_epi32(__A, __B),
(__v4si)__W); (__v4si)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_srli_epi32(__mmask8 __U, __m128i __A, int __B) _mm_maskz_srli_epi32(__mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U,
(__v4si)_mm_srli_epi32(__A, __B), (__v4si)_mm_srli_epi32(__A, __B),
(__v4si)_mm_setzero_si128()); (__v4si)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_srli_epi32(__m256i __W, __mmask8 __U, __m256i __A, int __B) _mm256_mask_srli_epi32(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_srli_epi32(__A, __B), (__v8si)_mm256_srli_epi32(__A, __B),
(__v8si)__W); (__v8si)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_srli_epi32(__mmask8 __U, __m256i __A, int __B) _mm256_maskz_srli_epi32(__mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_srli_epi32(__A, __B), (__v8si)_mm256_srli_epi32(__A, __B),
(__v8si)_mm256_setzero_si256()); (__v8si)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srl_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) _mm_mask_srl_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B)
Show All 23 Lines
_mm256_maskz_srl_epi64(__mmask8 __U, __m256i __A, __m128i __B) _mm256_maskz_srl_epi64(__mmask8 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U,
(__v4di)_mm256_srl_epi64(__A, __B), (__v4di)_mm256_srl_epi64(__A, __B),
(__v4di)_mm256_setzero_si256()); (__v4di)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srli_epi64(__m128i __W, __mmask8 __U, __m128i __A, int __B) _mm_mask_srli_epi64(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U,
(__v2di)_mm_srli_epi64(__A, __B), (__v2di)_mm_srli_epi64(__A, __B),
(__v2di)__W); (__v2di)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_srli_epi64(__mmask8 __U, __m128i __A, int __B) _mm_maskz_srli_epi64(__mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U,
(__v2di)_mm_srli_epi64(__A, __B), (__v2di)_mm_srli_epi64(__A, __B),
(__v2di)_mm_setzero_si128()); (__v2di)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_srli_epi64(__m256i __W, __mmask8 __U, __m256i __A, int __B) _mm256_mask_srli_epi64(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U,
(__v4di)_mm256_srli_epi64(__A, __B), (__v4di)_mm256_srli_epi64(__A, __B),
(__v4di)__W); (__v4di)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_srli_epi64(__mmask8 __U, __m256i __A, int __B) _mm256_maskz_srli_epi64(__mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U,
(__v4di)_mm256_srli_epi64(__A, __B), (__v4di)_mm256_srli_epi64(__A, __B),
(__v4di)_mm256_setzero_si256()); (__v4di)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srav_epi32(__m128i __W, __mmask8 __U, __m128i __X, __m128i __Y) _mm_mask_srav_epi32(__m128i __W, __mmask8 __U, __m128i __X, __m128i __Y)
▲ Show 20 Lines • Show All 1,434 Lines • ▼ Show 20 Lines
_mm256_maskz_sra_epi32(__mmask8 __U, __m256i __A, __m128i __B) _mm256_maskz_sra_epi32(__mmask8 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_sra_epi32(__A, __B), (__v8si)_mm256_sra_epi32(__A, __B),
(__v8si)_mm256_setzero_si256()); (__v8si)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srai_epi32(__m128i __W, __mmask8 __U, __m128i __A, int __B) _mm_mask_srai_epi32(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U,
(__v4si)_mm_srai_epi32(__A, __B), (__v4si)_mm_srai_epi32(__A, __B),
(__v4si)__W); (__v4si)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_srai_epi32(__mmask8 __U, __m128i __A, int __B) _mm_maskz_srai_epi32(__mmask8 __U, __m128i __A, unsigned int __B)
{ {
return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U, return (__m128i)__builtin_ia32_selectd_128((__mmask8)__U,
(__v4si)_mm_srai_epi32(__A, __B), (__v4si)_mm_srai_epi32(__A, __B),
(__v4si)_mm_setzero_si128()); (__v4si)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_srai_epi32(__m256i __W, __mmask8 __U, __m256i __A, int __B) _mm256_mask_srai_epi32(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_srai_epi32(__A, __B), (__v8si)_mm256_srai_epi32(__A, __B),
(__v8si)__W); (__v8si)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_srai_epi32(__mmask8 __U, __m256i __A, int __B) _mm256_maskz_srai_epi32(__mmask8 __U, __m256i __A, unsigned int __B)
{ {
return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U, return (__m256i)__builtin_ia32_selectd_256((__mmask8)__U,
(__v8si)_mm256_srai_epi32(__A, __B), (__v8si)_mm256_srai_epi32(__A, __B),
(__v8si)_mm256_setzero_si256()); (__v8si)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_sra_epi64(__m128i __A, __m128i __B) _mm_sra_epi64(__m128i __A, __m128i __B)
Show All 35 Lines
_mm256_maskz_sra_epi64(__mmask8 __U, __m256i __A, __m128i __B) _mm256_maskz_sra_epi64(__mmask8 __U, __m256i __A, __m128i __B)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, \ return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, \
(__v4di)_mm256_sra_epi64(__A, __B), \ (__v4di)_mm256_sra_epi64(__A, __B), \
(__v4di)_mm256_setzero_si256()); (__v4di)_mm256_setzero_si256());
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_srai_epi64(__m128i __A, int __imm) _mm_srai_epi64(__m128i __A, unsigned int __imm)
{ {
return (__m128i)__builtin_ia32_psraqi128((__v2di)__A, __imm); return (__m128i)__builtin_ia32_psraqi128((__v2di)__A, __imm);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_mask_srai_epi64(__m128i __W, __mmask8 __U, __m128i __A, int __imm) _mm_mask_srai_epi64(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __imm)
{ {
return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, \ return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, \
(__v2di)_mm_srai_epi64(__A, __imm), \ (__v2di)_mm_srai_epi64(__A, __imm), \
(__v2di)__W); (__v2di)__W);
} }
static __inline__ __m128i __DEFAULT_FN_ATTRS128 static __inline__ __m128i __DEFAULT_FN_ATTRS128
_mm_maskz_srai_epi64(__mmask8 __U, __m128i __A, int __imm) _mm_maskz_srai_epi64(__mmask8 __U, __m128i __A, unsigned int __imm)
{ {
return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, \ return (__m128i)__builtin_ia32_selectq_128((__mmask8)__U, \
(__v2di)_mm_srai_epi64(__A, __imm), \ (__v2di)_mm_srai_epi64(__A, __imm), \
(__v2di)_mm_setzero_si128()); (__v2di)_mm_setzero_si128());
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_srai_epi64(__m256i __A, int __imm) _mm256_srai_epi64(__m256i __A, unsigned int __imm)
{ {
return (__m256i)__builtin_ia32_psraqi256((__v4di)__A, __imm); return (__m256i)__builtin_ia32_psraqi256((__v4di)__A, __imm);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_mask_srai_epi64(__m256i __W, __mmask8 __U, __m256i __A, int __imm) _mm256_mask_srai_epi64(__m256i __W, __mmask8 __U, __m256i __A,
unsigned int __imm)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, \ return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, \
(__v4di)_mm256_srai_epi64(__A, __imm), \ (__v4di)_mm256_srai_epi64(__A, __imm), \
(__v4di)__W); (__v4di)__W);
} }
static __inline__ __m256i __DEFAULT_FN_ATTRS256 static __inline__ __m256i __DEFAULT_FN_ATTRS256
_mm256_maskz_srai_epi64(__mmask8 __U, __m256i __A, int __imm) _mm256_maskz_srai_epi64(__mmask8 __U, __m256i __A, unsigned int __imm)
{ {
return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, \ return (__m256i)__builtin_ia32_selectq_256((__mmask8)__U, \
(__v4di)_mm256_srai_epi64(__A, __imm), \ (__v4di)_mm256_srai_epi64(__A, __imm), \
(__v4di)_mm256_setzero_si256()); (__v4di)_mm256_setzero_si256());
} }
#define _mm_ternarylogic_epi32(A, B, C, imm) \ #define _mm_ternarylogic_epi32(A, B, C, imm) \
(__m128i)__builtin_ia32_pternlogd128_mask((__v4si)(__m128i)(A), \ (__m128i)__builtin_ia32_pternlogd128_mask((__v4si)(__m128i)(A), \
▲ Show 20 Lines • Show All 1,916 Lines • Show Last 20 Lines

clang/test/CodeGen/avx512bw-builtins.c

// RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512bw -emit-llvm -o - -Wall -Werror | FileCheck %s // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512bw -emit-llvm -o - -Wall -Werror -Wsign-conversion | FileCheck %s
// RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512bw -fno-signed-char -emit-llvm -o - -Wall -Werror | FileCheck %s // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512bw -fno-signed-char -emit-llvm -o - -Wall -Werror -Wsign-conversion | FileCheck %s
#include <immintrin.h> #include <immintrin.h>
__mmask32 test_knot_mask32(__mmask32 a) { __mmask32 test_knot_mask32(__mmask32 a) {
// CHECK-LABEL: @test_knot_mask32 // CHECK-LABEL: @test_knot_mask32
// CHECK: [[IN:%.*]] = bitcast i32 %{{.*}} to <32 x i1> // CHECK: [[IN:%.*]] = bitcast i32 %{{.*}} to <32 x i1>
// CHECK: [[NOT:%.*]] = xor <32 x i1> [[IN]], <i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true> // CHECK: [[NOT:%.*]] = xor <32 x i1> [[IN]], <i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true, i1 true>
▲ Show 20 Lines • Show All 1,706 Lines • ▼ Show 20 Lines
} }
__m512i test_mm512_slli_epi16(__m512i __A) { __m512i test_mm512_slli_epi16(__m512i __A) {
// CHECK-LABEL: @test_mm512_slli_epi16 // CHECK-LABEL: @test_mm512_slli_epi16
// CHECK: @llvm.x86.avx512.pslli.w.512 // CHECK: @llvm.x86.avx512.pslli.w.512
return _mm512_slli_epi16(__A, 5); return _mm512_slli_epi16(__A, 5);
} }
__m512i test_mm512_slli_epi16_2(__m512i __A, int __B) { __m512i test_mm512_slli_epi16_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_slli_epi16_2 // CHECK-LABEL: @test_mm512_slli_epi16_2
// CHECK: @llvm.x86.avx512.pslli.w.512 // CHECK: @llvm.x86.avx512.pslli.w.512
return _mm512_slli_epi16(__A, __B); return _mm512_slli_epi16(__A, __B);
} }
__m512i test_mm512_mask_slli_epi16(__m512i __W, __mmask32 __U, __m512i __A) { __m512i test_mm512_mask_slli_epi16(__m512i __W, __mmask32 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_slli_epi16 // CHECK-LABEL: @test_mm512_mask_slli_epi16
// CHECK: @llvm.x86.avx512.pslli.w.512 // CHECK: @llvm.x86.avx512.pslli.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_slli_epi16(__W, __U, __A, 5); return _mm512_mask_slli_epi16(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_slli_epi16_2(__m512i __W, __mmask32 __U, __m512i __A, int __B) { __m512i test_mm512_mask_slli_epi16_2(__m512i __W, __mmask32 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_slli_epi16_2 // CHECK-LABEL: @test_mm512_mask_slli_epi16_2
// CHECK: @llvm.x86.avx512.pslli.w.512 // CHECK: @llvm.x86.avx512.pslli.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_slli_epi16(__W, __U, __A, __B); return _mm512_mask_slli_epi16(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_slli_epi16(__mmask32 __U, __m512i __A) { __m512i test_mm512_maskz_slli_epi16(__mmask32 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_slli_epi16 // CHECK-LABEL: @test_mm512_maskz_slli_epi16
// CHECK: @llvm.x86.avx512.pslli.w.512 // CHECK: @llvm.x86.avx512.pslli.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_maskz_slli_epi16(__U, __A, 5); return _mm512_maskz_slli_epi16(__U, __A, 5);
} }
__m512i test_mm512_maskz_slli_epi16_2(__mmask32 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_slli_epi16_2(__mmask32 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_slli_epi16_2 // CHECK-LABEL: @test_mm512_maskz_slli_epi16_2
// CHECK: @llvm.x86.avx512.pslli.w.512 // CHECK: @llvm.x86.avx512.pslli.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_maskz_slli_epi16(__U, __A, __B); return _mm512_maskz_slli_epi16(__U, __A, __B);
} }
__m512i test_mm512_bslli_epi128(__m512i __A) { __m512i test_mm512_bslli_epi128(__m512i __A) {
// CHECK-LABEL: @test_mm512_bslli_epi128 // CHECK-LABEL: @test_mm512_bslli_epi128
▲ Show 20 Lines • Show All 62 Lines • ▼ Show 20 Lines
} }
__m512i test_mm512_srai_epi16(__m512i __A) { __m512i test_mm512_srai_epi16(__m512i __A) {
// CHECK-LABEL: @test_mm512_srai_epi16 // CHECK-LABEL: @test_mm512_srai_epi16
// CHECK: @llvm.x86.avx512.psrai.w.512 // CHECK: @llvm.x86.avx512.psrai.w.512
return _mm512_srai_epi16(__A, 5); return _mm512_srai_epi16(__A, 5);
} }
__m512i test_mm512_srai_epi16_2(__m512i __A, int __B) { __m512i test_mm512_srai_epi16_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_srai_epi16_2 // CHECK-LABEL: @test_mm512_srai_epi16_2
// CHECK: @llvm.x86.avx512.psrai.w.512 // CHECK: @llvm.x86.avx512.psrai.w.512
return _mm512_srai_epi16(__A, __B); return _mm512_srai_epi16(__A, __B);
} }
__m512i test_mm512_mask_srai_epi16(__m512i __W, __mmask32 __U, __m512i __A) { __m512i test_mm512_mask_srai_epi16(__m512i __W, __mmask32 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_srai_epi16 // CHECK-LABEL: @test_mm512_mask_srai_epi16
// CHECK: @llvm.x86.avx512.psrai.w.512 // CHECK: @llvm.x86.avx512.psrai.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_srai_epi16(__W, __U, __A, 5); return _mm512_mask_srai_epi16(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_srai_epi16_2(__m512i __W, __mmask32 __U, __m512i __A, int __B) { __m512i test_mm512_mask_srai_epi16_2(__m512i __W, __mmask32 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_srai_epi16_2 // CHECK-LABEL: @test_mm512_mask_srai_epi16_2
// CHECK: @llvm.x86.avx512.psrai.w.512 // CHECK: @llvm.x86.avx512.psrai.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_srai_epi16(__W, __U, __A, __B); return _mm512_mask_srai_epi16(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_srai_epi16(__mmask32 __U, __m512i __A) { __m512i test_mm512_maskz_srai_epi16(__mmask32 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_srai_epi16 // CHECK-LABEL: @test_mm512_maskz_srai_epi16
// CHECK: @llvm.x86.avx512.psrai.w.512 // CHECK: @llvm.x86.avx512.psrai.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_maskz_srai_epi16(__U, __A, 5); return _mm512_maskz_srai_epi16(__U, __A, 5);
} }
__m512i test_mm512_maskz_srai_epi16_2(__mmask32 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_srai_epi16_2(__mmask32 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_srai_epi16_2 // CHECK-LABEL: @test_mm512_maskz_srai_epi16_2
// CHECK: @llvm.x86.avx512.psrai.w.512 // CHECK: @llvm.x86.avx512.psrai.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_maskz_srai_epi16(__U, __A, __B); return _mm512_maskz_srai_epi16(__U, __A, __B);
} }
__m512i test_mm512_srl_epi16(__m512i __A, __m128i __B) { __m512i test_mm512_srl_epi16(__m512i __A, __m128i __B) {
// CHECK-LABEL: @test_mm512_srl_epi16 // CHECK-LABEL: @test_mm512_srl_epi16
Show All 16 Lines
} }
__m512i test_mm512_srli_epi16(__m512i __A) { __m512i test_mm512_srli_epi16(__m512i __A) {
// CHECK-LABEL: @test_mm512_srli_epi16 // CHECK-LABEL: @test_mm512_srli_epi16
// CHECK: @llvm.x86.avx512.psrli.w.512 // CHECK: @llvm.x86.avx512.psrli.w.512
return _mm512_srli_epi16(__A, 5); return _mm512_srli_epi16(__A, 5);
} }
__m512i test_mm512_srli_epi16_2(__m512i __A, int __B) { __m512i test_mm512_srli_epi16_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_srli_epi16_2 // CHECK-LABEL: @test_mm512_srli_epi16_2
// CHECK: @llvm.x86.avx512.psrli.w.512 // CHECK: @llvm.x86.avx512.psrli.w.512
return _mm512_srli_epi16(__A, __B); return _mm512_srli_epi16(__A, __B);
} }
__m512i test_mm512_mask_srli_epi16(__m512i __W, __mmask32 __U, __m512i __A) { __m512i test_mm512_mask_srli_epi16(__m512i __W, __mmask32 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_srli_epi16 // CHECK-LABEL: @test_mm512_mask_srli_epi16
// CHECK: @llvm.x86.avx512.psrli.w.512 // CHECK: @llvm.x86.avx512.psrli.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_srli_epi16(__W, __U, __A, 5); return _mm512_mask_srli_epi16(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_srli_epi16_2(__m512i __W, __mmask32 __U, __m512i __A, int __B) { __m512i test_mm512_mask_srli_epi16_2(__m512i __W, __mmask32 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_srli_epi16_2 // CHECK-LABEL: @test_mm512_mask_srli_epi16_2
// CHECK: @llvm.x86.avx512.psrli.w.512 // CHECK: @llvm.x86.avx512.psrli.w.512
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}} // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_srli_epi16(__W, __U, __A, __B); return _mm512_mask_srli_epi16(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_srli_epi16(__mmask32 __U, __m512i __A) { __m512i test_mm512_maskz_srli_epi16(__mmask32 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_srli_epi16 // CHECK-LABEL: @test_mm512_maskz_srli_epi16
▲ Show 20 Lines • Show All 551 Lines • Show Last 20 Lines

clang/test/CodeGen/avx512f-builtins.c

  • This file is larger than 256 KB, so syntax highlighting is disabled by default.
// RUN: %clang_cc1 -fexperimental-new-pass-manager -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512f -emit-llvm -o - -Wall -Werror | FileCheck %s // RUN: %clang_cc1 -fexperimental-new-pass-manager -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512f -emit-llvm -o - -Wall -Werror -Wsign-conversion | FileCheck %s
// RUN: %clang_cc1 -fexperimental-new-pass-manager -flax-vector-conversions=none -fms-extensions -fms-compatibility -ffreestanding %s -triple=x86_64-windows-msvc -target-feature +avx512f -emit-llvm -o - -Wall -Werror | FileCheck %s // RUN: %clang_cc1 -fexperimental-new-pass-manager -flax-vector-conversions=none -fms-extensions -fms-compatibility -ffreestanding %s -triple=x86_64-windows-msvc -target-feature +avx512f -emit-llvm -o - -Wall -Werror -Wsign-conversion | FileCheck %s
#include <immintrin.h> #include <immintrin.h>
__m512d test_mm512_sqrt_pd(__m512d a) __m512d test_mm512_sqrt_pd(__m512d a)
{ {
// CHECK-LABEL: @test_mm512_sqrt_pd // CHECK-LABEL: @test_mm512_sqrt_pd
// CHECK: call <8 x double> @llvm.sqrt.v8f64(<8 x double> %{{.*}}) // CHECK: call <8 x double> @llvm.sqrt.v8f64(<8 x double> %{{.*}})
return _mm512_sqrt_pd(a); return _mm512_sqrt_pd(a);
▲ Show 20 Lines • Show All 4,154 Lines • ▼ Show 20 Lines
} }
__m512i test_mm512_slli_epi32(__m512i __A) { __m512i test_mm512_slli_epi32(__m512i __A) {
// CHECK-LABEL: @test_mm512_slli_epi32 // CHECK-LABEL: @test_mm512_slli_epi32
// CHECK: @llvm.x86.avx512.pslli.d.512 // CHECK: @llvm.x86.avx512.pslli.d.512
return _mm512_slli_epi32(__A, 5); return _mm512_slli_epi32(__A, 5);
} }
__m512i test_mm512_slli_epi32_2(__m512i __A, int __B) { __m512i test_mm512_slli_epi32_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_slli_epi32_2 // CHECK-LABEL: @test_mm512_slli_epi32_2
// CHECK: @llvm.x86.avx512.pslli.d.512 // CHECK: @llvm.x86.avx512.pslli.d.512
return _mm512_slli_epi32(__A, __B); return _mm512_slli_epi32(__A, __B);
} }
__m512i test_mm512_mask_slli_epi32(__m512i __W, __mmask16 __U, __m512i __A) { __m512i test_mm512_mask_slli_epi32(__m512i __W, __mmask16 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_slli_epi32 // CHECK-LABEL: @test_mm512_mask_slli_epi32
// CHECK: @llvm.x86.avx512.pslli.d.512 // CHECK: @llvm.x86.avx512.pslli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_mask_slli_epi32(__W, __U, __A, 5); return _mm512_mask_slli_epi32(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_slli_epi32_2(__m512i __W, __mmask16 __U, __m512i __A, int __B) { __m512i test_mm512_mask_slli_epi32_2(__m512i __W, __mmask16 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_slli_epi32_2 // CHECK-LABEL: @test_mm512_mask_slli_epi32_2
// CHECK: @llvm.x86.avx512.pslli.d.512 // CHECK: @llvm.x86.avx512.pslli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_mask_slli_epi32(__W, __U, __A, __B); return _mm512_mask_slli_epi32(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_slli_epi32(__mmask16 __U, __m512i __A) { __m512i test_mm512_maskz_slli_epi32(__mmask16 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_slli_epi32 // CHECK-LABEL: @test_mm512_maskz_slli_epi32
// CHECK: @llvm.x86.avx512.pslli.d.512 // CHECK: @llvm.x86.avx512.pslli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_maskz_slli_epi32(__U, __A, 5); return _mm512_maskz_slli_epi32(__U, __A, 5);
} }
__m512i test_mm512_maskz_slli_epi32_2(__mmask16 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_slli_epi32_2(__mmask16 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_slli_epi32_2 // CHECK-LABEL: @test_mm512_maskz_slli_epi32_2
// CHECK: @llvm.x86.avx512.pslli.d.512 // CHECK: @llvm.x86.avx512.pslli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_maskz_slli_epi32(__U, __A, __B); return _mm512_maskz_slli_epi32(__U, __A, __B);
} }
__m512i test_mm512_slli_epi64(__m512i __A) { __m512i test_mm512_slli_epi64(__m512i __A) {
// CHECK-LABEL: @test_mm512_slli_epi64 // CHECK-LABEL: @test_mm512_slli_epi64
// CHECK: @llvm.x86.avx512.pslli.q.512 // CHECK: @llvm.x86.avx512.pslli.q.512
return _mm512_slli_epi64(__A, 5); return _mm512_slli_epi64(__A, 5);
} }
__m512i test_mm512_slli_epi64_2(__m512i __A, int __B) { __m512i test_mm512_slli_epi64_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_slli_epi64_2 // CHECK-LABEL: @test_mm512_slli_epi64_2
// CHECK: @llvm.x86.avx512.pslli.q.512 // CHECK: @llvm.x86.avx512.pslli.q.512
return _mm512_slli_epi64(__A, __B); return _mm512_slli_epi64(__A, __B);
} }
__m512i test_mm512_mask_slli_epi64(__m512i __W, __mmask8 __U, __m512i __A) { __m512i test_mm512_mask_slli_epi64(__m512i __W, __mmask8 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_slli_epi64 // CHECK-LABEL: @test_mm512_mask_slli_epi64
// CHECK: @llvm.x86.avx512.pslli.q.512 // CHECK: @llvm.x86.avx512.pslli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_mask_slli_epi64(__W, __U, __A, 5); return _mm512_mask_slli_epi64(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_slli_epi64_2(__m512i __W, __mmask8 __U, __m512i __A, int __B) { __m512i test_mm512_mask_slli_epi64_2(__m512i __W, __mmask8 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_slli_epi64_2 // CHECK-LABEL: @test_mm512_mask_slli_epi64_2
// CHECK: @llvm.x86.avx512.pslli.q.512 // CHECK: @llvm.x86.avx512.pslli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_mask_slli_epi64(__W, __U, __A, __B); return _mm512_mask_slli_epi64(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_slli_epi64(__mmask8 __U, __m512i __A) { __m512i test_mm512_maskz_slli_epi64(__mmask8 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_slli_epi64 // CHECK-LABEL: @test_mm512_maskz_slli_epi64
// CHECK: @llvm.x86.avx512.pslli.q.512 // CHECK: @llvm.x86.avx512.pslli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_maskz_slli_epi64(__U, __A, 5); return _mm512_maskz_slli_epi64(__U, __A, 5);
} }
__m512i test_mm512_maskz_slli_epi64_2(__mmask8 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_slli_epi64_2(__mmask8 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_slli_epi64_2 // CHECK-LABEL: @test_mm512_maskz_slli_epi64_2
// CHECK: @llvm.x86.avx512.pslli.q.512 // CHECK: @llvm.x86.avx512.pslli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_maskz_slli_epi64(__U, __A, __B); return _mm512_maskz_slli_epi64(__U, __A, __B);
} }
__m512i test_mm512_srli_epi32(__m512i __A) { __m512i test_mm512_srli_epi32(__m512i __A) {
// CHECK-LABEL: @test_mm512_srli_epi32 // CHECK-LABEL: @test_mm512_srli_epi32
// CHECK: @llvm.x86.avx512.psrli.d.512 // CHECK: @llvm.x86.avx512.psrli.d.512
return _mm512_srli_epi32(__A, 5); return _mm512_srli_epi32(__A, 5);
} }
__m512i test_mm512_srli_epi32_2(__m512i __A, int __B) { __m512i test_mm512_srli_epi32_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_srli_epi32_2 // CHECK-LABEL: @test_mm512_srli_epi32_2
// CHECK: @llvm.x86.avx512.psrli.d.512 // CHECK: @llvm.x86.avx512.psrli.d.512
return _mm512_srli_epi32(__A, __B); return _mm512_srli_epi32(__A, __B);
} }
__m512i test_mm512_mask_srli_epi32(__m512i __W, __mmask16 __U, __m512i __A) { __m512i test_mm512_mask_srli_epi32(__m512i __W, __mmask16 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_srli_epi32 // CHECK-LABEL: @test_mm512_mask_srli_epi32
// CHECK: @llvm.x86.avx512.psrli.d.512 // CHECK: @llvm.x86.avx512.psrli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_mask_srli_epi32(__W, __U, __A, 5); return _mm512_mask_srli_epi32(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_srli_epi32_2(__m512i __W, __mmask16 __U, __m512i __A, int __B) { __m512i test_mm512_mask_srli_epi32_2(__m512i __W, __mmask16 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_srli_epi32_2 // CHECK-LABEL: @test_mm512_mask_srli_epi32_2
// CHECK: @llvm.x86.avx512.psrli.d.512 // CHECK: @llvm.x86.avx512.psrli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_mask_srli_epi32(__W, __U, __A, __B); return _mm512_mask_srli_epi32(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_srli_epi32(__mmask16 __U, __m512i __A) { __m512i test_mm512_maskz_srli_epi32(__mmask16 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_srli_epi32 // CHECK-LABEL: @test_mm512_maskz_srli_epi32
// CHECK: @llvm.x86.avx512.psrli.d.512 // CHECK: @llvm.x86.avx512.psrli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_maskz_srli_epi32(__U, __A, 5); return _mm512_maskz_srli_epi32(__U, __A, 5);
} }
__m512i test_mm512_maskz_srli_epi32_2(__mmask16 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_srli_epi32_2(__mmask16 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_srli_epi32_2 // CHECK-LABEL: @test_mm512_maskz_srli_epi32_2
// CHECK: @llvm.x86.avx512.psrli.d.512 // CHECK: @llvm.x86.avx512.psrli.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_maskz_srli_epi32(__U, __A, __B); return _mm512_maskz_srli_epi32(__U, __A, __B);
} }
__m512i test_mm512_srli_epi64(__m512i __A) { __m512i test_mm512_srli_epi64(__m512i __A) {
// CHECK-LABEL: @test_mm512_srli_epi64 // CHECK-LABEL: @test_mm512_srli_epi64
// CHECK: @llvm.x86.avx512.psrli.q.512 // CHECK: @llvm.x86.avx512.psrli.q.512
return _mm512_srli_epi64(__A, 5); return _mm512_srli_epi64(__A, 5);
} }
__m512i test_mm512_srli_epi64_2(__m512i __A, int __B) { __m512i test_mm512_srli_epi64_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_srli_epi64_2 // CHECK-LABEL: @test_mm512_srli_epi64_2
// CHECK: @llvm.x86.avx512.psrli.q.512 // CHECK: @llvm.x86.avx512.psrli.q.512
return _mm512_srli_epi64(__A, __B); return _mm512_srli_epi64(__A, __B);
} }
__m512i test_mm512_mask_srli_epi64(__m512i __W, __mmask8 __U, __m512i __A) { __m512i test_mm512_mask_srli_epi64(__m512i __W, __mmask8 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_srli_epi64 // CHECK-LABEL: @test_mm512_mask_srli_epi64
// CHECK: @llvm.x86.avx512.psrli.q.512 // CHECK: @llvm.x86.avx512.psrli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_mask_srli_epi64(__W, __U, __A, 5); return _mm512_mask_srli_epi64(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_srli_epi64_2(__m512i __W, __mmask8 __U, __m512i __A, int __B) { __m512i test_mm512_mask_srli_epi64_2(__m512i __W, __mmask8 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_srli_epi64_2 // CHECK-LABEL: @test_mm512_mask_srli_epi64_2
// CHECK: @llvm.x86.avx512.psrli.q.512 // CHECK: @llvm.x86.avx512.psrli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_mask_srli_epi64(__W, __U, __A, __B); return _mm512_mask_srli_epi64(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_srli_epi64(__mmask8 __U, __m512i __A) { __m512i test_mm512_maskz_srli_epi64(__mmask8 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_srli_epi64 // CHECK-LABEL: @test_mm512_maskz_srli_epi64
// CHECK: @llvm.x86.avx512.psrli.q.512 // CHECK: @llvm.x86.avx512.psrli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_maskz_srli_epi64(__U, __A, 5); return _mm512_maskz_srli_epi64(__U, __A, 5);
} }
__m512i test_mm512_maskz_srli_epi64_2(__mmask8 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_srli_epi64_2(__mmask8 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_srli_epi64_2 // CHECK-LABEL: @test_mm512_maskz_srli_epi64_2
// CHECK: @llvm.x86.avx512.psrli.q.512 // CHECK: @llvm.x86.avx512.psrli.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_maskz_srli_epi64(__U, __A, __B); return _mm512_maskz_srli_epi64(__U, __A, __B);
} }
__m512i test_mm512_mask_load_epi32(__m512i __W, __mmask16 __U, void const *__P) { __m512i test_mm512_mask_load_epi32(__m512i __W, __mmask16 __U, void const *__P) {
// CHECK-LABEL: @test_mm512_mask_load_epi32 // CHECK-LABEL: @test_mm512_mask_load_epi32
▲ Show 20 Lines • Show All 287 Lines • ▼ Show 20 Lines
__m512d test_mm512_mask_unpackhi_pd(__m512d __W, __mmask8 __U, __m512d __A, __m512d __B) { __m512d test_mm512_mask_unpackhi_pd(__m512d __W, __mmask8 __U, __m512d __A, __m512d __B) {
// CHECK-LABEL: @test_mm512_mask_unpackhi_pd // CHECK-LABEL: @test_mm512_mask_unpackhi_pd
// CHECK: shufflevector <8 x double> %{{.*}}, <8 x double> %{{.*}}, <8 x i32> <i32 1, i32 9, i32 3, i32 11, i32 5, i32 13, i32 7, i32 15> // CHECK: shufflevector <8 x double> %{{.*}}, <8 x double> %{{.*}}, <8 x i32> <i32 1, i32 9, i32 3, i32 11, i32 5, i32 13, i32 7, i32 15>
// CHECK: select <8 x i1> %{{.*}}, <8 x double> %{{.*}}, <8 x double> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x double> %{{.*}}, <8 x double> %{{.*}}
return _mm512_mask_unpackhi_pd(__W, __U, __A, __B); return _mm512_mask_unpackhi_pd(__W, __U, __A, __B);
} }
#if __x86_64__ #if __x86_64__
unsigned long long test_mm_cvt_roundsd_si64(__m128d __A) { long long test_mm_cvt_roundsd_si64(__m128d __A) {
// CHECK-LABEL: @test_mm_cvt_roundsd_si64 // CHECK-LABEL: @test_mm_cvt_roundsd_si64
// CHECK: @llvm.x86.avx512.vcvtsd2si64 // CHECK: @llvm.x86.avx512.vcvtsd2si64
return _mm_cvt_roundsd_si64(__A, _MM_FROUND_TO_ZERO | _MM_FROUND_NO_EXC); return _mm_cvt_roundsd_si64(__A, _MM_FROUND_TO_ZERO | _MM_FROUND_NO_EXC);
} }
#endif #endif
__m512i test_mm512_mask2_permutex2var_epi32(__m512i __A, __m512i __I, __mmask16 __U, __m512i __B) { __m512i test_mm512_mask2_permutex2var_epi32(__m512i __A, __m512i __I, __mmask16 __U, __m512i __B) {
// CHECK-LABEL: @test_mm512_mask2_permutex2var_epi32 // CHECK-LABEL: @test_mm512_mask2_permutex2var_epi32
// CHECK: @llvm.x86.avx512.vpermi2var.d.512 // CHECK: @llvm.x86.avx512.vpermi2var.d.512
▲ Show 20 Lines • Show All 183 Lines • ▼ Show 20 Lines
int test_mm_cvttsd_i32(__m128d __A) { int test_mm_cvttsd_i32(__m128d __A) {
// CHECK-LABEL: @test_mm_cvttsd_i32 // CHECK-LABEL: @test_mm_cvttsd_i32
// CHECK: @llvm.x86.avx512.cvttsd2si // CHECK: @llvm.x86.avx512.cvttsd2si
return _mm_cvttsd_i32(__A); return _mm_cvttsd_i32(__A);
} }
#ifdef __x86_64__ #ifdef __x86_64__
unsigned long long test_mm_cvtt_roundsd_si64(__m128d __A) { long long test_mm_cvtt_roundsd_si64(__m128d __A) {
// CHECK-LABEL: @test_mm_cvtt_roundsd_si64 // CHECK-LABEL: @test_mm_cvtt_roundsd_si64
// CHECK: @llvm.x86.avx512.cvttsd2si64 // CHECK: @llvm.x86.avx512.cvttsd2si64
return _mm_cvtt_roundsd_si64(__A, _MM_FROUND_NO_EXC); return _mm_cvtt_roundsd_si64(__A, _MM_FROUND_NO_EXC);
} }
long long test_mm_cvtt_roundsd_i64(__m128d __A) { long long test_mm_cvtt_roundsd_i64(__m128d __A) {
// CHECK-LABEL: @test_mm_cvtt_roundsd_i64 // CHECK-LABEL: @test_mm_cvtt_roundsd_i64
// CHECK: @llvm.x86.avx512.cvttsd2si64 // CHECK: @llvm.x86.avx512.cvttsd2si64
▲ Show 20 Lines • Show All 853 Lines • ▼ Show 20 Lines
} }
__m512i test_mm512_srai_epi32(__m512i __A) { __m512i test_mm512_srai_epi32(__m512i __A) {
// CHECK-LABEL: @test_mm512_srai_epi32 // CHECK-LABEL: @test_mm512_srai_epi32
// CHECK: @llvm.x86.avx512.psrai.d.512 // CHECK: @llvm.x86.avx512.psrai.d.512
return _mm512_srai_epi32(__A, 5); return _mm512_srai_epi32(__A, 5);
} }
__m512i test_mm512_srai_epi32_2(__m512i __A, int __B) { __m512i test_mm512_srai_epi32_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_srai_epi32_2 // CHECK-LABEL: @test_mm512_srai_epi32_2
// CHECK: @llvm.x86.avx512.psrai.d.512 // CHECK: @llvm.x86.avx512.psrai.d.512
return _mm512_srai_epi32(__A, __B); return _mm512_srai_epi32(__A, __B);
} }
__m512i test_mm512_mask_srai_epi32(__m512i __W, __mmask16 __U, __m512i __A) { __m512i test_mm512_mask_srai_epi32(__m512i __W, __mmask16 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_srai_epi32 // CHECK-LABEL: @test_mm512_mask_srai_epi32
// CHECK: @llvm.x86.avx512.psrai.d.512 // CHECK: @llvm.x86.avx512.psrai.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_mask_srai_epi32(__W, __U, __A, 5); return _mm512_mask_srai_epi32(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_srai_epi32_2(__m512i __W, __mmask16 __U, __m512i __A, int __B) { __m512i test_mm512_mask_srai_epi32_2(__m512i __W, __mmask16 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_srai_epi32_2 // CHECK-LABEL: @test_mm512_mask_srai_epi32_2
// CHECK: @llvm.x86.avx512.psrai.d.512 // CHECK: @llvm.x86.avx512.psrai.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_mask_srai_epi32(__W, __U, __A, __B); return _mm512_mask_srai_epi32(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_srai_epi32(__mmask16 __U, __m512i __A) { __m512i test_mm512_maskz_srai_epi32(__mmask16 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_srai_epi32 // CHECK-LABEL: @test_mm512_maskz_srai_epi32
// CHECK: @llvm.x86.avx512.psrai.d.512 // CHECK: @llvm.x86.avx512.psrai.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_maskz_srai_epi32(__U, __A, 5); return _mm512_maskz_srai_epi32(__U, __A, 5);
} }
__m512i test_mm512_maskz_srai_epi32_2(__mmask16 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_srai_epi32_2(__mmask16 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_srai_epi32_2 // CHECK-LABEL: @test_mm512_maskz_srai_epi32_2
// CHECK: @llvm.x86.avx512.psrai.d.512 // CHECK: @llvm.x86.avx512.psrai.d.512
// CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
return _mm512_maskz_srai_epi32(__U, __A, __B); return _mm512_maskz_srai_epi32(__U, __A, __B);
} }
__m512i test_mm512_srai_epi64(__m512i __A) { __m512i test_mm512_srai_epi64(__m512i __A) {
// CHECK-LABEL: @test_mm512_srai_epi64 // CHECK-LABEL: @test_mm512_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.512 // CHECK: @llvm.x86.avx512.psrai.q.512
return _mm512_srai_epi64(__A, 5); return _mm512_srai_epi64(__A, 5);
} }
__m512i test_mm512_srai_epi64_2(__m512i __A, int __B) { __m512i test_mm512_srai_epi64_2(__m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_srai_epi64_2 // CHECK-LABEL: @test_mm512_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.512 // CHECK: @llvm.x86.avx512.psrai.q.512
return _mm512_srai_epi64(__A, __B); return _mm512_srai_epi64(__A, __B);
} }
__m512i test_mm512_mask_srai_epi64(__m512i __W, __mmask8 __U, __m512i __A) { __m512i test_mm512_mask_srai_epi64(__m512i __W, __mmask8 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_mask_srai_epi64 // CHECK-LABEL: @test_mm512_mask_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.512 // CHECK: @llvm.x86.avx512.psrai.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_mask_srai_epi64(__W, __U, __A, 5); return _mm512_mask_srai_epi64(__W, __U, __A, 5);
} }
__m512i test_mm512_mask_srai_epi64_2(__m512i __W, __mmask8 __U, __m512i __A, int __B) { __m512i test_mm512_mask_srai_epi64_2(__m512i __W, __mmask8 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_mask_srai_epi64_2 // CHECK-LABEL: @test_mm512_mask_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.512 // CHECK: @llvm.x86.avx512.psrai.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_mask_srai_epi64(__W, __U, __A, __B); return _mm512_mask_srai_epi64(__W, __U, __A, __B);
} }
__m512i test_mm512_maskz_srai_epi64(__mmask8 __U, __m512i __A) { __m512i test_mm512_maskz_srai_epi64(__mmask8 __U, __m512i __A) {
// CHECK-LABEL: @test_mm512_maskz_srai_epi64 // CHECK-LABEL: @test_mm512_maskz_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.512 // CHECK: @llvm.x86.avx512.psrai.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_maskz_srai_epi64(__U, __A, 5); return _mm512_maskz_srai_epi64(__U, __A, 5);
} }
__m512i test_mm512_maskz_srai_epi64_2(__mmask8 __U, __m512i __A, int __B) { __m512i test_mm512_maskz_srai_epi64_2(__mmask8 __U, __m512i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm512_maskz_srai_epi64_2 // CHECK-LABEL: @test_mm512_maskz_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.512 // CHECK: @llvm.x86.avx512.psrai.q.512
// CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
return _mm512_maskz_srai_epi64(__U, __A, __B); return _mm512_maskz_srai_epi64(__U, __A, __B);
} }
__m512i test_mm512_sll_epi32(__m512i __A, __m128i __B) { __m512i test_mm512_sll_epi32(__m512i __A, __m128i __B) {
// CHECK-LABEL: @test_mm512_sll_epi32 // CHECK-LABEL: @test_mm512_sll_epi32
▲ Show 20 Lines • Show All 5,084 Lines • Show Last 20 Lines

clang/test/CodeGen/avx512vl-builtins.c

  • This file is larger than 256 KB, so syntax highlighting is disabled by default.
// RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -fexperimental-new-pass-manager -triple=x86_64-apple-darwin -target-feature +avx512f -target-feature +avx512vl -emit-llvm -o - -Wall -Werror | FileCheck %s // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -fexperimental-new-pass-manager -triple=x86_64-apple-darwin -target-feature +avx512f -target-feature +avx512vl -emit-llvm -o - -Wall -Werror -Wsign-conversion | FileCheck %s
#include <immintrin.h> #include <immintrin.h>
__mmask8 test_mm_cmpeq_epu32_mask(__m128i __a, __m128i __b) { __mmask8 test_mm_cmpeq_epu32_mask(__m128i __a, __m128i __b) {
// CHECK-LABEL: @test_mm_cmpeq_epu32_mask // CHECK-LABEL: @test_mm_cmpeq_epu32_mask
// CHECK: icmp eq <4 x i32> %{{.*}}, %{{.*}} // CHECK: icmp eq <4 x i32> %{{.*}}, %{{.*}}
// CHECK: shufflevector <4 x i1> %{{.*}}, <4 x i1> zeroinitializer, <8 x i32> <i32 0, i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7> // CHECK: shufflevector <4 x i1> %{{.*}}, <4 x i1> zeroinitializer, <8 x i32> <i32 0, i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7>
return (__mmask8)_mm_cmpeq_epu32_mask(__a, __b); return (__mmask8)_mm_cmpeq_epu32_mask(__a, __b);
▲ Show 20 Lines • Show All 6,221 Lines • ▼ Show 20 Lines
__m128i test_mm_mask_srli_epi32(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_srli_epi32(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_srli_epi32 // CHECK-LABEL: @test_mm_mask_srli_epi32
// CHECK: @llvm.x86.sse2.psrli.d // CHECK: @llvm.x86.sse2.psrli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_srli_epi32(__W, __U, __A, 5); return _mm_mask_srli_epi32(__W, __U, __A, 5);
} }
__m128i test_mm_mask_srli_epi32_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_srli_epi32_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_srli_epi32_2 // CHECK-LABEL: @test_mm_mask_srli_epi32_2
// CHECK: @llvm.x86.sse2.psrli.d // CHECK: @llvm.x86.sse2.psrli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_srli_epi32(__W, __U, __A, __B); return _mm_mask_srli_epi32(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_srli_epi32(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_srli_epi32(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_srli_epi32 // CHECK-LABEL: @test_mm_maskz_srli_epi32
// CHECK: @llvm.x86.sse2.psrli.d // CHECK: @llvm.x86.sse2.psrli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_maskz_srli_epi32(__U, __A, 5); return _mm_maskz_srli_epi32(__U, __A, 5);
} }
__m128i test_mm_maskz_srli_epi32_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_srli_epi32_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_srli_epi32_2 // CHECK-LABEL: @test_mm_maskz_srli_epi32_2
// CHECK: @llvm.x86.sse2.psrli.d // CHECK: @llvm.x86.sse2.psrli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_maskz_srli_epi32(__U, __A, __B); return _mm_maskz_srli_epi32(__U, __A, __B);
} }
__m256i test_mm256_mask_srli_epi32(__m256i __W, __mmask8 __U, __m256i __A) { __m256i test_mm256_mask_srli_epi32(__m256i __W, __mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_srli_epi32 // CHECK-LABEL: @test_mm256_mask_srli_epi32
// CHECK: @llvm.x86.avx2.psrli.d // CHECK: @llvm.x86.avx2.psrli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_mask_srli_epi32(__W, __U, __A, 5); return _mm256_mask_srli_epi32(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_srli_epi32_2(__m256i __W, __mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_mask_srli_epi32_2(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_srli_epi32_2 // CHECK-LABEL: @test_mm256_mask_srli_epi32_2
// CHECK: @llvm.x86.avx2.psrli.d // CHECK: @llvm.x86.avx2.psrli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_mask_srli_epi32(__W, __U, __A, __B); return _mm256_mask_srli_epi32(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_srli_epi32(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_srli_epi32(__mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_srli_epi32 // CHECK-LABEL: @test_mm256_maskz_srli_epi32
// CHECK: @llvm.x86.avx2.psrli.d // CHECK: @llvm.x86.avx2.psrli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_maskz_srli_epi32(__U, __A, 5); return _mm256_maskz_srli_epi32(__U, __A, 5);
} }
__m256i test_mm256_maskz_srli_epi32_2(__mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_maskz_srli_epi32_2(__mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_srli_epi32_2 // CHECK-LABEL: @test_mm256_maskz_srli_epi32_2
// CHECK: @llvm.x86.avx2.psrli.d // CHECK: @llvm.x86.avx2.psrli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_maskz_srli_epi32(__U, __A, __B); return _mm256_maskz_srli_epi32(__U, __A, __B);
} }
__m128i test_mm_mask_srl_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) { __m128i test_mm_mask_srl_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) {
// CHECK-LABEL: @test_mm_mask_srl_epi64 // CHECK-LABEL: @test_mm_mask_srl_epi64
// CHECK: @llvm.x86.sse2.psrl.q // CHECK: @llvm.x86.sse2.psrl.q
Show All 24 Lines
__m128i test_mm_mask_srli_epi64(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_srli_epi64(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_srli_epi64 // CHECK-LABEL: @test_mm_mask_srli_epi64
// CHECK: @llvm.x86.sse2.psrli.q // CHECK: @llvm.x86.sse2.psrli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_mask_srli_epi64(__W, __U, __A, 5); return _mm_mask_srli_epi64(__W, __U, __A, 5);
} }
__m128i test_mm_mask_srli_epi64_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_srli_epi64_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_srli_epi64_2 // CHECK-LABEL: @test_mm_mask_srli_epi64_2
// CHECK: @llvm.x86.sse2.psrli.q // CHECK: @llvm.x86.sse2.psrli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_mask_srli_epi64(__W, __U, __A, __B); return _mm_mask_srli_epi64(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_srli_epi64(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_srli_epi64(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_srli_epi64 // CHECK-LABEL: @test_mm_maskz_srli_epi64
// CHECK: @llvm.x86.sse2.psrli.q // CHECK: @llvm.x86.sse2.psrli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_maskz_srli_epi64(__U, __A, 5); return _mm_maskz_srli_epi64(__U, __A, 5);
} }
__m128i test_mm_maskz_srli_epi64_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_srli_epi64_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_srli_epi64_2 // CHECK-LABEL: @test_mm_maskz_srli_epi64_2
// CHECK: @llvm.x86.sse2.psrli.q // CHECK: @llvm.x86.sse2.psrli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_maskz_srli_epi64(__U, __A, __B); return _mm_maskz_srli_epi64(__U, __A, __B);
} }
__m256i test_mm256_mask_srli_epi64(__m256i __W, __mmask8 __U, __m256i __A) { __m256i test_mm256_mask_srli_epi64(__m256i __W, __mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_srli_epi64 // CHECK-LABEL: @test_mm256_mask_srli_epi64
// CHECK: @llvm.x86.avx2.psrli.q // CHECK: @llvm.x86.avx2.psrli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_mask_srli_epi64(__W, __U, __A, 5); return _mm256_mask_srli_epi64(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_srli_epi64_2(__m256i __W, __mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_mask_srli_epi64_2(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_srli_epi64_2 // CHECK-LABEL: @test_mm256_mask_srli_epi64_2
// CHECK: @llvm.x86.avx2.psrli.q // CHECK: @llvm.x86.avx2.psrli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_mask_srli_epi64(__W, __U, __A, __B); return _mm256_mask_srli_epi64(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_srli_epi64(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_srli_epi64(__mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_srli_epi64 // CHECK-LABEL: @test_mm256_maskz_srli_epi64
// CHECK: @llvm.x86.avx2.psrli.q // CHECK: @llvm.x86.avx2.psrli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_maskz_srli_epi64(__U, __A, 5); return _mm256_maskz_srli_epi64(__U, __A, 5);
} }
__m256i test_mm256_maskz_srli_epi64_2(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_srli_epi64_2(__mmask8 __U,__m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_srli_epi64_2 // CHECK-LABEL: @test_mm256_maskz_srli_epi64_2
// CHECK: @llvm.x86.avx2.psrli.q // CHECK: @llvm.x86.avx2.psrli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_maskz_srli_epi64(__U, __A, 5); return _mm256_maskz_srli_epi64(__U, __A, __B);
} }
__m128i test_mm_mask_sll_epi32(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) { __m128i test_mm_mask_sll_epi32(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) {
// CHECK-LABEL: @test_mm_mask_sll_epi32 // CHECK-LABEL: @test_mm_mask_sll_epi32
// CHECK: @llvm.x86.sse2.psll.d // CHECK: @llvm.x86.sse2.psll.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_sll_epi32(__W, __U, __A, __B); return _mm_mask_sll_epi32(__W, __U, __A, __B);
} }
Show All 21 Lines
__m128i test_mm_mask_slli_epi32(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_slli_epi32(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_slli_epi32 // CHECK-LABEL: @test_mm_mask_slli_epi32
// CHECK: @llvm.x86.sse2.pslli.d // CHECK: @llvm.x86.sse2.pslli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_slli_epi32(__W, __U, __A, 5); return _mm_mask_slli_epi32(__W, __U, __A, 5);
} }
__m128i test_mm_mask_slli_epi32_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_slli_epi32_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_slli_epi32_2 // CHECK-LABEL: @test_mm_mask_slli_epi32_2
// CHECK: @llvm.x86.sse2.pslli.d // CHECK: @llvm.x86.sse2.pslli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_slli_epi32(__W, __U, __A, __B); return _mm_mask_slli_epi32(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_slli_epi32(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_slli_epi32(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_slli_epi32 // CHECK-LABEL: @test_mm_maskz_slli_epi32
// CHECK: @llvm.x86.sse2.pslli.d // CHECK: @llvm.x86.sse2.pslli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_maskz_slli_epi32(__U, __A, 5); return _mm_maskz_slli_epi32(__U, __A, 5);
} }
__m128i test_mm_maskz_slli_epi32_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_slli_epi32_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_slli_epi32_2 // CHECK-LABEL: @test_mm_maskz_slli_epi32_2
// CHECK: @llvm.x86.sse2.pslli.d // CHECK: @llvm.x86.sse2.pslli.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_maskz_slli_epi32(__U, __A, __B); return _mm_maskz_slli_epi32(__U, __A, __B);
} }
__m256i test_mm256_mask_slli_epi32(__m256i __W, __mmask8 __U, __m256i __A) { __m256i test_mm256_mask_slli_epi32(__m256i __W, __mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_slli_epi32 // CHECK-LABEL: @test_mm256_mask_slli_epi32
// CHECK: @llvm.x86.avx2.pslli.d // CHECK: @llvm.x86.avx2.pslli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_mask_slli_epi32(__W, __U, __A, 5); return _mm256_mask_slli_epi32(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_slli_epi32_2(__m256i __W, __mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_mask_slli_epi32_2(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_slli_epi32_2 // CHECK-LABEL: @test_mm256_mask_slli_epi32_2
// CHECK: @llvm.x86.avx2.pslli.d // CHECK: @llvm.x86.avx2.pslli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_mask_slli_epi32(__W, __U, __A, __B); return _mm256_mask_slli_epi32(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_slli_epi32(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_slli_epi32(__mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_slli_epi32 // CHECK-LABEL: @test_mm256_maskz_slli_epi32
// CHECK: @llvm.x86.avx2.pslli.d // CHECK: @llvm.x86.avx2.pslli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_maskz_slli_epi32(__U, __A, 5); return _mm256_maskz_slli_epi32(__U, __A, 5);
} }
__m256i test_mm256_maskz_slli_epi32_2(__mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_maskz_slli_epi32_2(__mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_slli_epi32_2 // CHECK-LABEL: @test_mm256_maskz_slli_epi32_2
// CHECK: @llvm.x86.avx2.pslli.d // CHECK: @llvm.x86.avx2.pslli.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_maskz_slli_epi32(__U, __A, __B); return _mm256_maskz_slli_epi32(__U, __A, __B);
} }
__m128i test_mm_mask_sll_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) { __m128i test_mm_mask_sll_epi64(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) {
// CHECK-LABEL: @test_mm_mask_sll_epi64 // CHECK-LABEL: @test_mm_mask_sll_epi64
Show All 25 Lines
__m128i test_mm_mask_slli_epi64(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_slli_epi64(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_slli_epi64 // CHECK-LABEL: @test_mm_mask_slli_epi64
// CHECK: @llvm.x86.sse2.pslli.q // CHECK: @llvm.x86.sse2.pslli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_mask_slli_epi64(__W, __U, __A, 5); return _mm_mask_slli_epi64(__W, __U, __A, 5);
} }
__m128i test_mm_mask_slli_epi64_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_slli_epi64_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_slli_epi64_2 // CHECK-LABEL: @test_mm_mask_slli_epi64_2
// CHECK: @llvm.x86.sse2.pslli.q // CHECK: @llvm.x86.sse2.pslli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_mask_slli_epi64(__W, __U, __A, __B); return _mm_mask_slli_epi64(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_slli_epi64(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_slli_epi64(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_slli_epi64 // CHECK-LABEL: @test_mm_maskz_slli_epi64
// CHECK: @llvm.x86.sse2.pslli.q // CHECK: @llvm.x86.sse2.pslli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_maskz_slli_epi64(__U, __A, 5); return _mm_maskz_slli_epi64(__U, __A, 5);
} }
__m128i test_mm_maskz_slli_epi64_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_slli_epi64_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_slli_epi64_2 // CHECK-LABEL: @test_mm_maskz_slli_epi64_2
// CHECK: @llvm.x86.sse2.pslli.q // CHECK: @llvm.x86.sse2.pslli.q
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_maskz_slli_epi64(__U, __A, __B); return _mm_maskz_slli_epi64(__U, __A, __B);
} }
__m256i test_mm256_mask_slli_epi64(__m256i __W, __mmask8 __U, __m256i __A) { __m256i test_mm256_mask_slli_epi64(__m256i __W, __mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_slli_epi64 // CHECK-LABEL: @test_mm256_mask_slli_epi64
// CHECK: @llvm.x86.avx2.pslli.q // CHECK: @llvm.x86.avx2.pslli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_mask_slli_epi64(__W, __U, __A, 5); return _mm256_mask_slli_epi64(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_slli_epi64_2(__m256i __W, __mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_mask_slli_epi64_2(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_slli_epi64_2 // CHECK-LABEL: @test_mm256_mask_slli_epi64_2
// CHECK: @llvm.x86.avx2.pslli.q // CHECK: @llvm.x86.avx2.pslli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_mask_slli_epi64(__W, __U, __A, __B); return _mm256_mask_slli_epi64(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_slli_epi64(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_slli_epi64(__mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_slli_epi64 // CHECK-LABEL: @test_mm256_maskz_slli_epi64
// CHECK: @llvm.x86.avx2.pslli.q // CHECK: @llvm.x86.avx2.pslli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_maskz_slli_epi64(__U, __A, 5); return _mm256_maskz_slli_epi64(__U, __A, 5);
} }
__m256i test_mm256_maskz_slli_epi64_2(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_slli_epi64_2(__mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_slli_epi64_2 // CHECK-LABEL: @test_mm256_maskz_slli_epi64_2
// CHECK: @llvm.x86.avx2.pslli.q // CHECK: @llvm.x86.avx2.pslli.q
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_maskz_slli_epi64(__U, __A, 5); return _mm256_maskz_slli_epi64(__U, __A, __B);
} }
__m128i test_mm_mask_srav_epi32(__m128i __W, __mmask8 __U, __m128i __X, __m128i __Y) { __m128i test_mm_mask_srav_epi32(__m128i __W, __mmask8 __U, __m128i __X, __m128i __Y) {
// CHECK-LABEL: @test_mm_mask_srav_epi32 // CHECK-LABEL: @test_mm_mask_srav_epi32
// CHECK: @llvm.x86.avx2.psrav.d // CHECK: @llvm.x86.avx2.psrav.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_srav_epi32(__W, __U, __X, __Y); return _mm_mask_srav_epi32(__W, __U, __X, __Y);
} }
▲ Show 20 Lines • Show All 1,239 Lines • ▼ Show 20 Lines
__m128i test_mm_mask_srai_epi32(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_srai_epi32(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_srai_epi32 // CHECK-LABEL: @test_mm_mask_srai_epi32
// CHECK: @llvm.x86.sse2.psrai.d // CHECK: @llvm.x86.sse2.psrai.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_srai_epi32(__W, __U, __A, 5); return _mm_mask_srai_epi32(__W, __U, __A, 5);
} }
__m128i test_mm_mask_srai_epi32_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_srai_epi32_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_srai_epi32_2 // CHECK-LABEL: @test_mm_mask_srai_epi32_2
// CHECK: @llvm.x86.sse2.psrai.d // CHECK: @llvm.x86.sse2.psrai.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_mask_srai_epi32(__W, __U, __A, __B); return _mm_mask_srai_epi32(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_srai_epi32(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_srai_epi32(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_srai_epi32 // CHECK-LABEL: @test_mm_maskz_srai_epi32
// CHECK: @llvm.x86.sse2.psrai.d // CHECK: @llvm.x86.sse2.psrai.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_maskz_srai_epi32(__U, __A, 5); return _mm_maskz_srai_epi32(__U, __A, 5);
} }
__m128i test_mm_maskz_srai_epi32_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_srai_epi32_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_srai_epi32_2 // CHECK-LABEL: @test_mm_maskz_srai_epi32_2
// CHECK: @llvm.x86.sse2.psrai.d // CHECK: @llvm.x86.sse2.psrai.d
// CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
return _mm_maskz_srai_epi32(__U, __A, __B); return _mm_maskz_srai_epi32(__U, __A, __B);
} }
__m256i test_mm256_mask_srai_epi32(__m256i __W, __mmask8 __U, __m256i __A) { __m256i test_mm256_mask_srai_epi32(__m256i __W, __mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_srai_epi32 // CHECK-LABEL: @test_mm256_mask_srai_epi32
// CHECK: @llvm.x86.avx2.psrai.d // CHECK: @llvm.x86.avx2.psrai.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_mask_srai_epi32(__W, __U, __A, 5); return _mm256_mask_srai_epi32(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_srai_epi32_2(__m256i __W, __mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_mask_srai_epi32_2(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_srai_epi32_2 // CHECK-LABEL: @test_mm256_mask_srai_epi32_2
// CHECK: @llvm.x86.avx2.psrai.d // CHECK: @llvm.x86.avx2.psrai.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_mask_srai_epi32(__W, __U, __A, __B); return _mm256_mask_srai_epi32(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_srai_epi32(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_srai_epi32(__mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_srai_epi32 // CHECK-LABEL: @test_mm256_maskz_srai_epi32
// CHECK: @llvm.x86.avx2.psrai.d // CHECK: @llvm.x86.avx2.psrai.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_maskz_srai_epi32(__U, __A, 5); return _mm256_maskz_srai_epi32(__U, __A, 5);
} }
__m256i test_mm256_maskz_srai_epi32_2(__mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_maskz_srai_epi32_2(__mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_srai_epi32_2 // CHECK-LABEL: @test_mm256_maskz_srai_epi32_2
// CHECK: @llvm.x86.avx2.psrai.d // CHECK: @llvm.x86.avx2.psrai.d
// CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
return _mm256_maskz_srai_epi32(__U, __A, __B); return _mm256_maskz_srai_epi32(__U, __A, __B);
} }
__m128i test_mm_sra_epi64(__m128i __A, __m128i __B) { __m128i test_mm_sra_epi64(__m128i __A, __m128i __B) {
// CHECK-LABEL: @test_mm_sra_epi64 // CHECK-LABEL: @test_mm_sra_epi64
Show All 36 Lines
} }
__m128i test_mm_srai_epi64(__m128i __A) { __m128i test_mm_srai_epi64(__m128i __A) {
// CHECK-LABEL: @test_mm_srai_epi64 // CHECK-LABEL: @test_mm_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.128 // CHECK: @llvm.x86.avx512.psrai.q.128
return _mm_srai_epi64(__A, 5); return _mm_srai_epi64(__A, 5);
} }
__m128i test_mm_srai_epi64_2(__m128i __A, int __B) { __m128i test_mm_srai_epi64_2(__m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_srai_epi64_2 // CHECK-LABEL: @test_mm_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.128 // CHECK: @llvm.x86.avx512.psrai.q.128
return _mm_srai_epi64(__A, __B); return _mm_srai_epi64(__A, __B);
} }
__m128i test_mm_mask_srai_epi64(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_srai_epi64(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_srai_epi64 // CHECK-LABEL: @test_mm_mask_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.128 // CHECK: @llvm.x86.avx512.psrai.q.128
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_mask_srai_epi64(__W, __U, __A, 5); return _mm_mask_srai_epi64(__W, __U, __A, 5);
} }
__m128i test_mm_mask_srai_epi64_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_srai_epi64_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_srai_epi64_2 // CHECK-LABEL: @test_mm_mask_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.128 // CHECK: @llvm.x86.avx512.psrai.q.128
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_mask_srai_epi64(__W, __U, __A, __B); return _mm_mask_srai_epi64(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_srai_epi64(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_srai_epi64(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_srai_epi64 // CHECK-LABEL: @test_mm_maskz_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.128 // CHECK: @llvm.x86.avx512.psrai.q.128
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_maskz_srai_epi64(__U, __A, 5); return _mm_maskz_srai_epi64(__U, __A, 5);
} }
__m128i test_mm_maskz_srai_epi64_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_srai_epi64_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_srai_epi64_2 // CHECK-LABEL: @test_mm_maskz_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.128 // CHECK: @llvm.x86.avx512.psrai.q.128
// CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
return _mm_maskz_srai_epi64(__U, __A, __B); return _mm_maskz_srai_epi64(__U, __A, __B);
} }
__m256i test_mm256_srai_epi64(__m256i __A) { __m256i test_mm256_srai_epi64(__m256i __A) {
// CHECK-LABEL: @test_mm256_srai_epi64 // CHECK-LABEL: @test_mm256_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.256 // CHECK: @llvm.x86.avx512.psrai.q.256
return _mm256_srai_epi64(__A, 5); return _mm256_srai_epi64(__A, 5);
} }
__m256i test_mm256_srai_epi64_2(__m256i __A, int __B) { __m256i test_mm256_srai_epi64_2(__m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_srai_epi64_2 // CHECK-LABEL: @test_mm256_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.256 // CHECK: @llvm.x86.avx512.psrai.q.256
return _mm256_srai_epi64(__A, __B); return _mm256_srai_epi64(__A, __B);
} }
__m256i test_mm256_mask_srai_epi64(__m256i __W, __mmask8 __U, __m256i __A) { __m256i test_mm256_mask_srai_epi64(__m256i __W, __mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_srai_epi64 // CHECK-LABEL: @test_mm256_mask_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.256 // CHECK: @llvm.x86.avx512.psrai.q.256
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_mask_srai_epi64(__W, __U, __A, 5); return _mm256_mask_srai_epi64(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_srai_epi64_2(__m256i __W, __mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_mask_srai_epi64_2(__m256i __W, __mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_srai_epi64_2 // CHECK-LABEL: @test_mm256_mask_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.256 // CHECK: @llvm.x86.avx512.psrai.q.256
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_mask_srai_epi64(__W, __U, __A, __B); return _mm256_mask_srai_epi64(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_srai_epi64(__mmask8 __U, __m256i __A) { __m256i test_mm256_maskz_srai_epi64(__mmask8 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_srai_epi64 // CHECK-LABEL: @test_mm256_maskz_srai_epi64
// CHECK: @llvm.x86.avx512.psrai.q.256 // CHECK: @llvm.x86.avx512.psrai.q.256
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_maskz_srai_epi64(__U, __A, 5); return _mm256_maskz_srai_epi64(__U, __A, 5);
} }
__m256i test_mm256_maskz_srai_epi64_2(__mmask8 __U, __m256i __A, int __B) { __m256i test_mm256_maskz_srai_epi64_2(__mmask8 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_srai_epi64_2 // CHECK-LABEL: @test_mm256_maskz_srai_epi64_2
// CHECK: @llvm.x86.avx512.psrai.q.256 // CHECK: @llvm.x86.avx512.psrai.q.256
// CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
return _mm256_maskz_srai_epi64(__U, __A, __B); return _mm256_maskz_srai_epi64(__U, __A, __B);
} }
__m128i test_mm_ternarylogic_epi32(__m128i __A, __m128i __B, __m128i __C) { __m128i test_mm_ternarylogic_epi32(__m128i __A, __m128i __B, __m128i __C) {
// CHECK-LABEL: @test_mm_ternarylogic_epi32 // CHECK-LABEL: @test_mm_ternarylogic_epi32
▲ Show 20 Lines • Show All 1,919 Lines • Show Last 20 Lines

clang/test/CodeGen/avx512vlbw-builtins.c

// RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -fexperimental-new-pass-manager -triple=x86_64-apple-darwin -target-feature +avx512bw -target-feature +avx512vl -emit-llvm -o - -Wall -Werror | FileCheck %s // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -fexperimental-new-pass-manager -triple=x86_64-apple-darwin -target-feature +avx512bw -target-feature +avx512vl -emit-llvm -o - -Wall -Werror -Wsign-conversion | FileCheck %s
// RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -fexperimental-new-pass-manager -triple=x86_64-apple-darwin -target-feature +avx512bw -target-feature +avx512vl -fno-signed-char -emit-llvm -o - -Wall -Werror | FileCheck %s // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -fexperimental-new-pass-manager -triple=x86_64-apple-darwin -target-feature +avx512bw -target-feature +avx512vl -fno-signed-char -emit-llvm -o - -Wall -Werror -Wsign-conversion | FileCheck %s
#include <immintrin.h> #include <immintrin.h>
__mmask32 test_mm256_cmpeq_epi8_mask(__m256i __a, __m256i __b) { __mmask32 test_mm256_cmpeq_epi8_mask(__m256i __a, __m256i __b) {
// CHECK-LABEL: @test_mm256_cmpeq_epi8_mask // CHECK-LABEL: @test_mm256_cmpeq_epi8_mask
// CHECK: icmp eq <32 x i8> %{{.*}}, %{{.*}} // CHECK: icmp eq <32 x i8> %{{.*}}, %{{.*}}
return (__mmask32)_mm256_cmpeq_epi8_mask(__a, __b); return (__mmask32)_mm256_cmpeq_epi8_mask(__a, __b);
} }
▲ Show 20 Lines • Show All 2,183 Lines • ▼ Show 20 Lines
__m128i test_mm_mask_slli_epi16(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_slli_epi16(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_slli_epi16 // CHECK-LABEL: @test_mm_mask_slli_epi16
// CHECK: @llvm.x86.sse2.pslli.w // CHECK: @llvm.x86.sse2.pslli.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_mask_slli_epi16(__W, __U, __A, 5); return _mm_mask_slli_epi16(__W, __U, __A, 5);
} }
__m128i test_mm_mask_slli_epi16_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_slli_epi16_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_slli_epi16_2 // CHECK-LABEL: @test_mm_mask_slli_epi16_2
// CHECK: @llvm.x86.sse2.pslli.w // CHECK: @llvm.x86.sse2.pslli.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_mask_slli_epi16(__W, __U, __A, __B); return _mm_mask_slli_epi16(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_slli_epi16(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_slli_epi16(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_slli_epi16 // CHECK-LABEL: @test_mm_maskz_slli_epi16
// CHECK: @llvm.x86.sse2.pslli.w // CHECK: @llvm.x86.sse2.pslli.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_maskz_slli_epi16(__U, __A, 5); return _mm_maskz_slli_epi16(__U, __A, 5);
} }
__m128i test_mm_maskz_slli_epi16_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_slli_epi16_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_slli_epi16_2 // CHECK-LABEL: @test_mm_maskz_slli_epi16_2
// CHECK: @llvm.x86.sse2.pslli.w // CHECK: @llvm.x86.sse2.pslli.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_maskz_slli_epi16(__U, __A, __B); return _mm_maskz_slli_epi16(__U, __A, __B);
} }
__m256i test_mm256_mask_slli_epi16(__m256i __W, __mmask16 __U, __m256i __A) { __m256i test_mm256_mask_slli_epi16(__m256i __W, __mmask16 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_slli_epi16 // CHECK-LABEL: @test_mm256_mask_slli_epi16
// CHECK: @llvm.x86.avx2.pslli.w // CHECK: @llvm.x86.avx2.pslli.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_mask_slli_epi16(__W, __U, __A, 5); return _mm256_mask_slli_epi16(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_slli_epi16_2(__m256i __W, __mmask16 __U, __m256i __A, int __B) { __m256i test_mm256_mask_slli_epi16_2(__m256i __W, __mmask16 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_slli_epi16_2 // CHECK-LABEL: @test_mm256_mask_slli_epi16_2
// CHECK: @llvm.x86.avx2.pslli.w // CHECK: @llvm.x86.avx2.pslli.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_mask_slli_epi16(__W, __U, __A, __B); return _mm256_mask_slli_epi16(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_slli_epi16(__mmask16 __U, __m256i __A) { __m256i test_mm256_maskz_slli_epi16(__mmask16 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_slli_epi16 // CHECK-LABEL: @test_mm256_maskz_slli_epi16
// CHECK: @llvm.x86.avx2.pslli.w // CHECK: @llvm.x86.avx2.pslli.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_maskz_slli_epi16(__U, __A, 5); return _mm256_maskz_slli_epi16(__U, __A, 5);
} }
__m256i test_mm256_maskz_slli_epi16_2(__mmask16 __U, __m256i __A, int __B) { __m256i test_mm256_maskz_slli_epi16_2(__mmask16 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_slli_epi16_2 // CHECK-LABEL: @test_mm256_maskz_slli_epi16_2
// CHECK: @llvm.x86.avx2.pslli.w // CHECK: @llvm.x86.avx2.pslli.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_maskz_slli_epi16(__U, __A, __B); return _mm256_maskz_slli_epi16(__U, __A, __B);
} }
__m256i test_mm256_srlv_epi16(__m256i __A, __m256i __B) { __m256i test_mm256_srlv_epi16(__m256i __A, __m256i __B) {
// CHECK-LABEL: @test_mm256_srlv_epi16 // CHECK-LABEL: @test_mm256_srlv_epi16
▲ Show 20 Lines • Show All 189 Lines • ▼ Show 20 Lines
__m128i test_mm_mask_srai_epi16(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_srai_epi16(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_srai_epi16 // CHECK-LABEL: @test_mm_mask_srai_epi16
// CHECK: @llvm.x86.sse2.psrai.w // CHECK: @llvm.x86.sse2.psrai.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_mask_srai_epi16(__W, __U, __A, 5); return _mm_mask_srai_epi16(__W, __U, __A, 5);
} }
__m128i test_mm_mask_srai_epi16_2(__m128i __W, __mmask8 __U, __m128i __A, int __B) { __m128i test_mm_mask_srai_epi16_2(__m128i __W, __mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_mask_srai_epi16_2 // CHECK-LABEL: @test_mm_mask_srai_epi16_2
// CHECK: @llvm.x86.sse2.psrai.w // CHECK: @llvm.x86.sse2.psrai.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_mask_srai_epi16(__W, __U, __A, __B); return _mm_mask_srai_epi16(__W, __U, __A, __B);
} }
__m128i test_mm_maskz_srai_epi16(__mmask8 __U, __m128i __A) { __m128i test_mm_maskz_srai_epi16(__mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_maskz_srai_epi16 // CHECK-LABEL: @test_mm_maskz_srai_epi16
// CHECK: @llvm.x86.sse2.psrai.w // CHECK: @llvm.x86.sse2.psrai.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_maskz_srai_epi16(__U, __A, 5); return _mm_maskz_srai_epi16(__U, __A, 5);
} }
__m128i test_mm_maskz_srai_epi16_2(__mmask8 __U, __m128i __A, int __B) { __m128i test_mm_maskz_srai_epi16_2(__mmask8 __U, __m128i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm_maskz_srai_epi16_2 // CHECK-LABEL: @test_mm_maskz_srai_epi16_2
// CHECK: @llvm.x86.sse2.psrai.w // CHECK: @llvm.x86.sse2.psrai.w
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}} // CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_maskz_srai_epi16(__U, __A, __B); return _mm_maskz_srai_epi16(__U, __A, __B);
} }
__m256i test_mm256_mask_srai_epi16(__m256i __W, __mmask16 __U, __m256i __A) { __m256i test_mm256_mask_srai_epi16(__m256i __W, __mmask16 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_mask_srai_epi16 // CHECK-LABEL: @test_mm256_mask_srai_epi16
// CHECK: @llvm.x86.avx2.psrai.w // CHECK: @llvm.x86.avx2.psrai.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_mask_srai_epi16(__W, __U, __A, 5); return _mm256_mask_srai_epi16(__W, __U, __A, 5);
} }
__m256i test_mm256_mask_srai_epi16_2(__m256i __W, __mmask16 __U, __m256i __A, int __B) { __m256i test_mm256_mask_srai_epi16_2(__m256i __W, __mmask16 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_mask_srai_epi16_2 // CHECK-LABEL: @test_mm256_mask_srai_epi16_2
// CHECK: @llvm.x86.avx2.psrai.w // CHECK: @llvm.x86.avx2.psrai.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_mask_srai_epi16(__W, __U, __A, __B); return _mm256_mask_srai_epi16(__W, __U, __A, __B);
} }
__m256i test_mm256_maskz_srai_epi16(__mmask16 __U, __m256i __A) { __m256i test_mm256_maskz_srai_epi16(__mmask16 __U, __m256i __A) {
// CHECK-LABEL: @test_mm256_maskz_srai_epi16 // CHECK-LABEL: @test_mm256_maskz_srai_epi16
// CHECK: @llvm.x86.avx2.psrai.w // CHECK: @llvm.x86.avx2.psrai.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_maskz_srai_epi16(__U, __A, 5); return _mm256_maskz_srai_epi16(__U, __A, 5);
} }
__m256i test_mm256_maskz_srai_epi16_2(__mmask16 __U, __m256i __A, int __B) { __m256i test_mm256_maskz_srai_epi16_2(__mmask16 __U, __m256i __A, unsigned int __B) {
// CHECK-LABEL: @test_mm256_maskz_srai_epi16_2 // CHECK-LABEL: @test_mm256_maskz_srai_epi16_2
// CHECK: @llvm.x86.avx2.psrai.w // CHECK: @llvm.x86.avx2.psrai.w
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}} // CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_maskz_srai_epi16(__U, __A, __B); return _mm256_maskz_srai_epi16(__U, __A, __B);
} }
__m128i test_mm_mask_mov_epi16(__m128i __W, __mmask8 __U, __m128i __A) { __m128i test_mm_mask_mov_epi16(__m128i __W, __mmask8 __U, __m128i __A) {
// CHECK-LABEL: @test_mm_mask_mov_epi16 // CHECK-LABEL: @test_mm_mask_mov_epi16
▲ Show 20 Lines • Show All 790 Lines • Show Last 20 Lines