Skip to content

Commit f050b79

Browse files
author
Igor Breger
committedMar 19, 2017
[X86][AVX512][Clang][Intrinsics] Adding missing intrinsics to Clang .
Summary: Adding missing intrinsics : _mm512_set_epi16, _mm512_set_epi8, _mm512_permutevar_epi32 _mm512_mask_permutevar_epi32 Reviewers: zvi, guyblank, eladcohen, craig.topper Reviewed By: craig.topper Subscribers: craig.topper, cfe-commits Differential Revision: https://reviews.llvm.org/D31034 llvm-svn: 298208
·
llvmorg-21-initllvmorg-5.0.0-rc1
1 parent 0ef61ec commit f050b79

File tree

2 files changed

+170
-0
lines changed

2 files changed

+170
-0
lines changed
 

‎clang/lib/Headers/avx512fintrin.h

Lines changed: 43 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -8848,6 +8848,8 @@ _mm512_permutexvar_epi32 (__m512i __X, __m512i __Y)
88488848
(__mmask16) -1);
88498849
}
88508850

8851+
#define _mm512_permutevar_epi32 _mm512_permutexvar_epi32
8852+
88518853
static __inline__ __m512i __DEFAULT_FN_ATTRS
88528854
_mm512_mask_permutexvar_epi32 (__m512i __W, __mmask16 __M, __m512i __X,
88538855
__m512i __Y)
@@ -8858,6 +8860,8 @@ _mm512_mask_permutexvar_epi32 (__m512i __W, __mmask16 __M, __m512i __X,
88588860
__M);
88598861
}
88608862

8863+
#define _mm512_mask_permutevar_epi32 _mm512_mask_permutexvar_epi32
8864+
88618865
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
88628866
_mm512_kand (__mmask16 __A, __mmask16 __B)
88638867
{
@@ -9625,6 +9629,45 @@ _mm512_mask_set1_epi64 (__m512i __O, __mmask8 __M, long long __A)
96259629
}
96269630
#endif
96279631

9632+
static __inline __m512i __DEFAULT_FN_ATTRS
9633+
_mm512_set_epi8 (char __e63, char __e62, char __e61, char __e60, char __e59,
9634+
char __e58, char __e57, char __e56, char __e55, char __e54, char __e53,
9635+
char __e52, char __e51, char __e50, char __e49, char __e48, char __e47,
9636+
char __e46, char __e45, char __e44, char __e43, char __e42, char __e41,
9637+
char __e40, char __e39, char __e38, char __e37, char __e36, char __e35,
9638+
char __e34, char __e33, char __e32, char __e31, char __e30, char __e29,
9639+
char __e28, char __e27, char __e26, char __e25, char __e24, char __e23,
9640+
char __e22, char __e21, char __e20, char __e19, char __e18, char __e17,
9641+
char __e16, char __e15, char __e14, char __e13, char __e12, char __e11,
9642+
char __e10, char __e9, char __e8, char __e7, char __e6, char __e5,
9643+
char __e4, char __e3, char __e2, char __e1, char __e0) {
9644+
9645+
return __extension__ (__m512i)(__v64qi)
9646+
{__e0, __e1, __e2, __e3, __e4, __e5, __e6, __e7,
9647+
__e8, __e9, __e10, __e11, __e12, __e13, __e14, __e15,
9648+
__e16, __e17, __e18, __e19, __e20, __e21, __e22, __e23,
9649+
__e24, __e25, __e26, __e27, __e28, __e29, __e30, __e31,
9650+
__e32, __e33, __e34, __e35, __e36, __e37, __e38, __e39,
9651+
__e40, __e41, __e42, __e43, __e44, __e45, __e46, __e47,
9652+
__e48, __e49, __e50, __e51, __e52, __e53, __e54, __e55,
9653+
__e56, __e57, __e58, __e59, __e60, __e61, __e62, __e63};
9654+
}
9655+
9656+
static __inline __m512i __DEFAULT_FN_ATTRS
9657+
_mm512_set_epi16(short __e31, short __e30, short __e29, short __e28,
9658+
short __e27, short __e26, short __e25, short __e24, short __e23,
9659+
short __e22, short __e21, short __e20, short __e19, short __e18,
9660+
short __e17, short __e16, short __e15, short __e14, short __e13,
9661+
short __e12, short __e11, short __e10, short __e9, short __e8,
9662+
short __e7, short __e6, short __e5, short __e4, short __e3,
9663+
short __e2, short __e1, short __e0) {
9664+
return __extension__ (__m512i)(__v32hi)
9665+
{__e0, __e1, __e2, __e3, __e4, __e5, __e6, __e7,
9666+
__e8, __e9, __e10, __e11, __e12, __e13, __e14, __e15,
9667+
__e16, __e17, __e18, __e19, __e20, __e21, __e22, __e23,
9668+
__e24, __e25, __e26, __e27, __e28, __e29, __e30, __e31 };
9669+
}
9670+
96289671
static __inline __m512i __DEFAULT_FN_ATTRS
96299672
_mm512_set_epi32 (int __A, int __B, int __C, int __D,
96309673
int __E, int __F, int __G, int __H,

‎clang/test/CodeGen/avx512f-builtins.c

Lines changed: 127 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -7712,6 +7712,133 @@ __m512i test_mm512_mask_set1_epi32 (__m512i __O, __mmask16 __M, int __A)
77127712
return _mm512_mask_set1_epi32 ( __O, __M, __A);
77137713
}
77147714

7715+
__m512i test_mm512_set_epi8(char e63, char e62, char e61, char e60, char e59,
7716+
char e58, char e57, char e56, char e55, char e54, char e53, char e52,
7717+
char e51, char e50, char e49, char e48, char e47, char e46, char e45,
7718+
char e44, char e43, char e42, char e41, char e40, char e39, char e38,
7719+
char e37, char e36, char e35, char e34, char e33, char e32, char e31,
7720+
char e30, char e29, char e28, char e27, char e26, char e25, char e24,
7721+
char e23, char e22, char e21, char e20, char e19, char e18, char e17,
7722+
char e16, char e15, char e14, char e13, char e12, char e11, char e10,
7723+
char e9, char e8, char e7, char e6, char e5, char e4, char e3, char e2,
7724+
char e1, char e0) {
7725+
7726+
//CHECK-LABEL: @test_mm512_set_epi8
7727+
//CHECK: load i8, i8* %e63.addr, align 1
7728+
//CHECK: load i8, i8* %e62.addr, align 1
7729+
//CHECK: load i8, i8* %e61.addr, align 1
7730+
//CHECK: load i8, i8* %e60.addr, align 1
7731+
//CHECK: load i8, i8* %e59.addr, align 1
7732+
//CHECK: load i8, i8* %e58.addr, align 1
7733+
//CHECK: load i8, i8* %e57.addr, align 1
7734+
//CHECK: load i8, i8* %e56.addr, align 1
7735+
//CHECK: load i8, i8* %e55.addr, align 1
7736+
//CHECK: load i8, i8* %e54.addr, align 1
7737+
//CHECK: load i8, i8* %e53.addr, align 1
7738+
//CHECK: load i8, i8* %e52.addr, align 1
7739+
//CHECK: load i8, i8* %e51.addr, align 1
7740+
//CHECK: load i8, i8* %e50.addr, align 1
7741+
//CHECK: load i8, i8* %e49.addr, align 1
7742+
//CHECK: load i8, i8* %e48.addr, align 1
7743+
//CHECK: load i8, i8* %e47.addr, align 1
7744+
//CHECK: load i8, i8* %e46.addr, align 1
7745+
//CHECK: load i8, i8* %e45.addr, align 1
7746+
//CHECK: load i8, i8* %e44.addr, align 1
7747+
//CHECK: load i8, i8* %e43.addr, align 1
7748+
//CHECK: load i8, i8* %e42.addr, align 1
7749+
//CHECK: load i8, i8* %e41.addr, align 1
7750+
//CHECK: load i8, i8* %e40.addr, align 1
7751+
//CHECK: load i8, i8* %e39.addr, align 1
7752+
//CHECK: load i8, i8* %e38.addr, align 1
7753+
//CHECK: load i8, i8* %e37.addr, align 1
7754+
//CHECK: load i8, i8* %e36.addr, align 1
7755+
//CHECK: load i8, i8* %e35.addr, align 1
7756+
//CHECK: load i8, i8* %e34.addr, align 1
7757+
//CHECK: load i8, i8* %e33.addr, align 1
7758+
//CHECK: load i8, i8* %e32.addr, align 1
7759+
//CHECK: load i8, i8* %e31.addr, align 1
7760+
//CHECK: load i8, i8* %e30.addr, align 1
7761+
//CHECK: load i8, i8* %e29.addr, align 1
7762+
//CHECK: load i8, i8* %e28.addr, align 1
7763+
//CHECK: load i8, i8* %e27.addr, align 1
7764+
//CHECK: load i8, i8* %e26.addr, align 1
7765+
//CHECK: load i8, i8* %e25.addr, align 1
7766+
//CHECK: load i8, i8* %e24.addr, align 1
7767+
//CHECK: load i8, i8* %e23.addr, align 1
7768+
//CHECK: load i8, i8* %e22.addr, align 1
7769+
//CHECK: load i8, i8* %e21.addr, align 1
7770+
//CHECK: load i8, i8* %e20.addr, align 1
7771+
//CHECK: load i8, i8* %e19.addr, align 1
7772+
//CHECK: load i8, i8* %e18.addr, align 1
7773+
//CHECK: load i8, i8* %e17.addr, align 1
7774+
//CHECK: load i8, i8* %e16.addr, align 1
7775+
//CHECK: load i8, i8* %e15.addr, align 1
7776+
//CHECK: load i8, i8* %e14.addr, align 1
7777+
//CHECK: load i8, i8* %e13.addr, align 1
7778+
//CHECK: load i8, i8* %e12.addr, align 1
7779+
//CHECK: load i8, i8* %e11.addr, align 1
7780+
//CHECK: load i8, i8* %e10.addr, align 1
7781+
//CHECK: load i8, i8* %e9.addr, align 1
7782+
//CHECK: load i8, i8* %e8.addr, align 1
7783+
//CHECK: load i8, i8* %e7.addr, align 1
7784+
//CHECK: load i8, i8* %e6.addr, align 1
7785+
//CHECK: load i8, i8* %e5.addr, align 1
7786+
//CHECK: load i8, i8* %e4.addr, align 1
7787+
//CHECK: load i8, i8* %e3.addr, align 1
7788+
//CHECK: load i8, i8* %e2.addr, align 1
7789+
//CHECK: load i8, i8* %e1.addr, align 1
7790+
//CHECK: load i8, i8* %e0.addr, align 1
7791+
return _mm512_set_epi8(e63, e62, e61, e60, e59, e58, e57, e56, e55, e54,
7792+
e53, e52, e51, e50, e49, e48,e47, e46, e45, e44, e43, e42, e41, e40,
7793+
e39, e38, e37, e36, e35, e34, e33, e32,e31, e30, e29, e28, e27, e26,
7794+
e25, e24, e23, e22, e21, e20, e19, e18, e17, e16, e15, e14, e13, e12,
7795+
e11, e10, e9, e8, e7, e6, e5, e4, e3, e2, e1, e0);
7796+
}
7797+
7798+
__m512i test_mm512_set_epi16(short e31, short e30, short e29, short e28,
7799+
short e27, short e26, short e25, short e24, short e23, short e22,
7800+
short e21, short e20, short e19, short e18, short e17,
7801+
short e16, short e15, short e14, short e13, short e12,
7802+
short e11, short e10, short e9, short e8, short e7,
7803+
short e6, short e5, short e4, short e3, short e2, short e1, short e0) {
7804+
//CHECK-LABEL: @test_mm512_set_epi16
7805+
//CHECK: insertelement{{.*}}i32 0
7806+
//CHECK: insertelement{{.*}}i32 1
7807+
//CHECK: insertelement{{.*}}i32 2
7808+
//CHECK: insertelement{{.*}}i32 3
7809+
//CHECK: insertelement{{.*}}i32 4
7810+
//CHECK: insertelement{{.*}}i32 5
7811+
//CHECK: insertelement{{.*}}i32 6
7812+
//CHECK: insertelement{{.*}}i32 7
7813+
//CHECK: insertelement{{.*}}i32 8
7814+
//CHECK: insertelement{{.*}}i32 9
7815+
//CHECK: insertelement{{.*}}i32 10
7816+
//CHECK: insertelement{{.*}}i32 11
7817+
//CHECK: insertelement{{.*}}i32 12
7818+
//CHECK: insertelement{{.*}}i32 13
7819+
//CHECK: insertelement{{.*}}i32 14
7820+
//CHECK: insertelement{{.*}}i32 15
7821+
//CHECK: insertelement{{.*}}i32 16
7822+
//CHECK: insertelement{{.*}}i32 17
7823+
//CHECK: insertelement{{.*}}i32 18
7824+
//CHECK: insertelement{{.*}}i32 19
7825+
//CHECK: insertelement{{.*}}i32 20
7826+
//CHECK: insertelement{{.*}}i32 21
7827+
//CHECK: insertelement{{.*}}i32 22
7828+
//CHECK: insertelement{{.*}}i32 23
7829+
//CHECK: insertelement{{.*}}i32 24
7830+
//CHECK: insertelement{{.*}}i32 25
7831+
//CHECK: insertelement{{.*}}i32 26
7832+
//CHECK: insertelement{{.*}}i32 27
7833+
//CHECK: insertelement{{.*}}i32 28
7834+
//CHECK: insertelement{{.*}}i32 29
7835+
//CHECK: insertelement{{.*}}i32 30
7836+
//CHECK: insertelement{{.*}}i32 31
7837+
return _mm512_set_epi16(e31, e30, e29, e28, e27, e26, e25, e24, e23, e22,
7838+
e21, e20, e19, e18, e17, e16, e15, e14, e13, e12, e11, e10, e9, e8, e7,
7839+
e6, e5, e4, e3, e2, e1, e0);
7840+
7841+
}
77157842
__m512i test_mm512_set_epi32 (int __A, int __B, int __C, int __D,
77167843
int __E, int __F, int __G, int __H,
77177844
int __I, int __J, int __K, int __L,

0 commit comments

Comments
 (0)
Please sign in to comment.