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

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
lib/
Headers/
avx512fintrin.h
avx512fintrin.h (revision 268910)
34 lines
test/
CodeGen/
avx512f-builtins.c
avx512f-builtins.c (revision 268910)
26 lines

Diff 56580

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,337 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,209 Lines • Show Last 20 Lines

test/CodeGen/avx512f-builtins.c

Show First 20 Lines • Show All 6,017 Lines • ▼ Show 20 Lines
__m512 test_mm512_maskz_min_ps (__mmask16 __U, __m512 __A, __m512 __B) __m512 test_mm512_maskz_min_ps (__mmask16 __U, __m512 __A, __m512 __B)
{ {
// CHECK-LABEL: @test_mm512_maskz_min_ps // CHECK-LABEL: @test_mm512_maskz_min_ps
// CHECK: @llvm.x86.avx512.mask.min.ps.512 // CHECK: @llvm.x86.avx512.mask.min.ps.512
return _mm512_maskz_min_ps (__U,__A,__B); return _mm512_maskz_min_ps (__U,__A,__B);
} }
__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);
}