This is an archive of the discontinued LLVM Phabricator instance.

Differential D20069

[Clang][AVX512] completing missing intrinsics for [vpabs] instruction set
ClosedPublic

Authored by m_zuckerman on May 9 2016, 7:44 AM.

Details

Reviewers
AsafBadouh
delena
igorb
Commits
rGbf05a4589e28: [Clang][AVX512] completing missing intrinsics for [vpabs] instruction set
rC269680: [Clang][AVX512] completing missing intrinsics for [vpabs] instruction set
rL269680: [Clang][AVX512] completing missing intrinsics for [vpabs] instruction set

Diff Detail

Repository
rL LLVM

Event Timeline

m_zuckerman updated this revision to Diff 56580.May 9 2016, 7:44 AM
m_zuckerman retitled this revision from to [Clang][AVX512] completing missing intrinsics for [vpabs] instruction set.
m_zuckerman updated this object.
m_zuckerman added reviewers: AsafBadouh, igorb, delena.
m_zuckerman added a subscriber: llvm-commits.
delena accepted this revision.May 15 2016, 5:40 AM
delena edited edge metadata.
This revision is now accepted and ready to land.May 15 2016, 5:40 AM
Closed by commit rL269680: [Clang][AVX512] completing missing intrinsics for [vpabs] instruction set (authored by mzuckerm). · Explain WhyMay 16 2016, 12:03 PM
This revision was automatically updated to reflect the committed changes.

Revision Contents

PathSize
cfe/
trunk/
lib/
Headers/
34 lines
test/
CodeGen/
27 lines

Diff 57381

cfe/trunk/lib/Headers/avx512fintrin.h

  • This file is larger than 256 KB, so syntax highlighting is disabled by default.
Show First 20 Lines • Show All 1,625 Lines • ▼ Show 20 Lines
_mm512_abs_epi64(__m512i __A) _mm512_abs_epi64(__m512i __A)
{ {
return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A, return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A,
(__v8di) (__v8di)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_abs_epi64 (__m512i __W, __mmask8 __U, __m512i __A)
{
return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A,
(__v8di) __W,
(__mmask8) __U);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_abs_epi64 (__mmask8 __U, __m512i __A)
{
return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A,
(__v8di)
_mm512_setzero_si512 (),
(__mmask8) __U);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_abs_epi32(__m512i __A) _mm512_abs_epi32(__m512i __A)
{ {
return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A, return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A,
(__v16si) (__v16si)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask16) -1); (__mmask16) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_abs_epi32 (__m512i __W, __mmask16 __U, __m512i __A)
{
return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A,
(__v16si) __W,
(__mmask16) __U);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_abs_epi32 (__mmask16 __U, __m512i __A)
{
return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A,
(__v16si)
_mm512_setzero_si512 (),
(__mmask16) __U);
}
static __inline__ __m128 __DEFAULT_FN_ATTRS static __inline__ __m128 __DEFAULT_FN_ATTRS
_mm_mask_add_ss(__m128 __W, __mmask8 __U,__m128 __A, __m128 __B) { _mm_mask_add_ss(__m128 __W, __mmask8 __U,__m128 __A, __m128 __B) {
return (__m128) __builtin_ia32_addss_round_mask ((__v4sf) __A, return (__m128) __builtin_ia32_addss_round_mask ((__v4sf) __A,
(__v4sf) __B, (__v4sf) __B,
(__v4sf) __W, (__v4sf) __W,
(__mmask8) __U, (__mmask8) __U,
_MM_FROUND_CUR_DIRECTION); _MM_FROUND_CUR_DIRECTION);
} }
▲ Show 20 Lines • Show All 7,504 Lines • Show Last 20 Lines

cfe/trunk/test/CodeGen/avx512f-builtins.c

Show First 20 Lines • Show All 6,568 Lines • ▼ Show 20 Lines__m512 test_mm512_set_ps (float __A, float __B, float __C, float __D,
//CHECK: insertelement{{.*}}i32 12 //CHECK: insertelement{{.*}}i32 12
//CHECK: insertelement{{.*}}i32 13 //CHECK: insertelement{{.*}}i32 13
//CHECK: insertelement{{.*}}i32 14 //CHECK: insertelement{{.*}}i32 14
//CHECK: insertelement{{.*}}i32 15 //CHECK: insertelement{{.*}}i32 15
return _mm512_set_ps( __A, __B, __C, __D, __E, __F, __G, __H, return _mm512_set_ps( __A, __B, __C, __D, __E, __F, __G, __H,
__I, __J, __K, __L, __M, __N, __O, __P); __I, __J, __K, __L, __M, __N, __O, __P);
} }
__m512i test_mm512_mask_abs_epi64 (__m512i __W, __mmask8 __U, __m512i __A)
{
// CHECK-LABEL: @test_mm512_mask_abs_epi64
// CHECK: @llvm.x86.avx512.mask.pabs.q.512
return _mm512_mask_abs_epi64 (__W,__U,__A);
}
__m512i test_mm512_maskz_abs_epi64 (__mmask8 __U, __m512i __A)
{
// CHECK-LABEL: @test_mm512_maskz_abs_epi64
// CHECK: @llvm.x86.avx512.mask.pabs.q.512
return _mm512_maskz_abs_epi64 (__U,__A);
}
__m512i test_mm512_mask_abs_epi32 (__m512i __W, __mmask16 __U, __m512i __A)
{
// CHECK-LABEL: @test_mm512_mask_abs_epi32
// CHECK: @llvm.x86.avx512.mask.pabs.d.512
return _mm512_mask_abs_epi32 (__W,__U,__A);
}
__m512i test_mm512_maskz_abs_epi32 (__mmask16 __U, __m512i __A)
{
// CHECK-LABEL: @test_mm512_maskz_abs_epi32
// CHECK: @llvm.x86.avx512.mask.pabs.d.512
return _mm512_maskz_abs_epi32 (__U,__A);
}