This is an archive of the discontinued LLVM Phabricator instance.

Differential D20064

[Clang][AVX512] completing missing intrinsics [vmin/vmax]{sd|sq|uq|ud}.
ClosedPublic

Authored by m_zuckerman on May 9 2016, 6:09 AM.

Details

Reviewers
AsafBadouh
delena
igorb
Commits
rGde860e558541: [Clang][AVX512] completing missing intrinsics [vmin/vmax]{sd|sq|uq|ud}.
rC269042: [Clang][AVX512] completing missing intrinsics [vmin/vmax]{sd|sq|uq|ud}.
rL269042: [Clang][AVX512] completing missing intrinsics [vmin/vmax]{sd|sq|uq|ud}.

Diff Detail

Repository
rL LLVM

Event Timeline

m_zuckerman updated this revision to Diff 56563.May 9 2016, 6:09 AM
m_zuckerman retitled this revision from to [Clang][AVX512] completing missing intrinsics [vmin/vmax]{sd|sq|uq|ud}..
m_zuckerman updated this object.
m_zuckerman added reviewers: AsafBadouh, igorb, delena.
m_zuckerman added a subscriber: llvm-commits.
AsafBadouh accepted this revision.May 10 2016, 1:05 AM
AsafBadouh edited edge metadata.

LGTM

This revision is now accepted and ready to land.May 10 2016, 1:05 AM
Closed by commit rL269042: [Clang][AVX512] completing missing intrinsics [vmin/vmax]{sd|sq|uq|ud}. (authored by mzuckerm). · Explain WhyMay 10 2016, 4:40 AM
This revision was automatically updated to reflect the committed changes.

Revision Contents

PathSize
cfe/
trunk/
lib/
Headers/
146 lines
test/
CodeGen/
113 lines

Diff 56691

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 842 Lines • ▼ Show 20 Lines
#define _mm_mask_max_round_sd(__W, __U, __A, __B, __R) __extension__ ({ \ #define _mm_mask_max_round_sd(__W, __U, __A, __B, __R) __extension__ ({ \
(__m128d) __builtin_ia32_maxsd_round_mask ((__v2df) __A, (__v2df) __B, \ (__m128d) __builtin_ia32_maxsd_round_mask ((__v2df) __A, (__v2df) __B, \
(__v2df) __W, (__mmask8) __U,__R); }) (__v2df) __W, (__mmask8) __U,__R); })
#define _mm_maskz_max_round_sd(__U, __A, __B, __R) __extension__ ({ \ #define _mm_maskz_max_round_sd(__U, __A, __B, __R) __extension__ ({ \
(__m128d) __builtin_ia32_maxsd_round_mask ((__v2df) __A, (__v2df) __B, \ (__m128d) __builtin_ia32_maxsd_round_mask ((__v2df) __A, (__v2df) __B, \
(__v2df) _mm_setzero_pd(), (__mmask8) __U,__R); }) (__v2df) _mm_setzero_pd(), (__mmask8) __U,__R); })
static __inline __m512i static __inline __m512i
__DEFAULT_FN_ATTRS __DEFAULT_FN_ATTRS
_mm512_max_epi32(__m512i __A, __m512i __B) _mm512_max_epi32(__m512i __A, __m512i __B)
{ {
return (__m512i) __builtin_ia32_pmaxsd512_mask ((__v16si) __A, return (__m512i) __builtin_ia32_pmaxsd512_mask ((__v16si) __A,
(__v16si) __B, (__v16si) __B,
(__v16si) (__v16si)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask16) -1); (__mmask16) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_max_epi32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxsd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_max_epi32 (__mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxsd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
_mm512_setzero_si512 (),
__M);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_max_epu32(__m512i __A, __m512i __B) _mm512_max_epu32(__m512i __A, __m512i __B)
{ {
return (__m512i) __builtin_ia32_pmaxud512_mask ((__v16si) __A, return (__m512i) __builtin_ia32_pmaxud512_mask ((__v16si) __A,
(__v16si) __B, (__v16si) __B,
(__v16si) (__v16si)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask16) -1); (__mmask16) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_max_epu32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxud512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_max_epu32 (__mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxud512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
_mm512_setzero_si512 (),
__M);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_max_epi64(__m512i __A, __m512i __B) _mm512_max_epi64(__m512i __A, __m512i __B)
{ {
return (__m512i) __builtin_ia32_pmaxsq512_mask ((__v8di) __A, return (__m512i) __builtin_ia32_pmaxsq512_mask ((__v8di) __A,
(__v8di) __B, (__v8di) __B,
(__v8di) (__v8di)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_max_epi64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxsq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_max_epi64 (__mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxsq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
_mm512_setzero_si512 (),
__M);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_max_epu64(__m512i __A, __m512i __B) _mm512_max_epu64(__m512i __A, __m512i __B)
{ {
return (__m512i) __builtin_ia32_pmaxuq512_mask ((__v8di) __A, return (__m512i) __builtin_ia32_pmaxuq512_mask ((__v8di) __A,
(__v8di) __B, (__v8di) __B,
(__v8di) (__v8di)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_max_epu64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxuq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_max_epu64 (__mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pmaxuq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
_mm512_setzero_si512 (),
__M);
}
static __inline__ __m512d __DEFAULT_FN_ATTRS static __inline__ __m512d __DEFAULT_FN_ATTRS
_mm512_min_pd(__m512d __A, __m512d __B) _mm512_min_pd(__m512d __A, __m512d __B)
{ {
return (__m512d) __builtin_ia32_minpd512_mask ((__v8df) __A, return (__m512d) __builtin_ia32_minpd512_mask ((__v8df) __A,
(__v8df) __B, (__v8df) __B,
(__v8df) (__v8df)
_mm512_setzero_pd (), _mm512_setzero_pd (),
(__mmask8) -1, (__mmask8) -1,
▲ Show 20 Lines • Show All 119 Lines • ▼ Show 20 Lines
{ {
return (__m512i) __builtin_ia32_pminsd512_mask ((__v16si) __A, return (__m512i) __builtin_ia32_pminsd512_mask ((__v16si) __A,
(__v16si) __B, (__v16si) __B,
(__v16si) (__v16si)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask16) -1); (__mmask16) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_min_epi32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminsd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_min_epi32 (__mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminsd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
_mm512_setzero_si512 (),
__M);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_min_epu32(__m512i __A, __m512i __B) _mm512_min_epu32(__m512i __A, __m512i __B)
{ {
return (__m512i) __builtin_ia32_pminud512_mask ((__v16si) __A, return (__m512i) __builtin_ia32_pminud512_mask ((__v16si) __A,
(__v16si) __B, (__v16si) __B,
(__v16si) (__v16si)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask16) -1); (__mmask16) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_min_epu32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminud512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_min_epu32 (__mmask16 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminud512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
_mm512_setzero_si512 (),
__M);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_min_epi64(__m512i __A, __m512i __B) _mm512_min_epi64(__m512i __A, __m512i __B)
{ {
return (__m512i) __builtin_ia32_pminsq512_mask ((__v8di) __A, return (__m512i) __builtin_ia32_pminsq512_mask ((__v8di) __A,
(__v8di) __B, (__v8di) __B,
(__v8di) (__v8di)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_min_epi64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminsq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_min_epi64 (__mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminsq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
_mm512_setzero_si512 (),
__M);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_min_epu64(__m512i __A, __m512i __B) _mm512_min_epu64(__m512i __A, __m512i __B)
{ {
return (__m512i) __builtin_ia32_pminuq512_mask ((__v8di) __A, return (__m512i) __builtin_ia32_pminuq512_mask ((__v8di) __A,
(__v8di) __B, (__v8di) __B,
(__v8di) (__v8di)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_mask_min_epu64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminuq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di) __W, __M);
}
static __inline__ __m512i __DEFAULT_FN_ATTRS
_mm512_maskz_min_epu64 (__mmask8 __M, __m512i __A, __m512i __B)
{
return (__m512i) __builtin_ia32_pminuq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
_mm512_setzero_si512 (),
__M);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_mm512_mul_epi32(__m512i __X, __m512i __Y) _mm512_mul_epi32(__m512i __X, __m512i __Y)
{ {
return (__m512i) __builtin_ia32_pmuldq512_mask ((__v16si) __X, return (__m512i) __builtin_ia32_pmuldq512_mask ((__v16si) __X,
(__v16si) __Y, (__v16si) __Y,
(__v8di) (__v8di)
_mm512_setzero_si512 (), _mm512_setzero_si512 (),
(__mmask8) -1); (__mmask8) -1);
▲ Show 20 Lines • Show All 7,596 Lines • Show Last 20 Lines

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

Show First 20 Lines • Show All 5,984 Lines • ▼ Show 20 Lines
__m512i test_mm512_mask_cvtps_epu32 (__m512i __W, __mmask16 __U, __m512 __A) __m512i test_mm512_mask_cvtps_epu32 (__m512i __W, __mmask16 __U, __m512 __A)
{ {
// CHECK-LABEL: @test_mm512_mask_cvtps_epu32 // CHECK-LABEL: @test_mm512_mask_cvtps_epu32
// CHECK: @llvm.x86.avx512.mask.cvtps2udq.512 // CHECK: @llvm.x86.avx512.mask.cvtps2udq.512
return _mm512_mask_cvtps_epu32( __W, __U, __A); return _mm512_mask_cvtps_epu32( __W, __U, __A);
} }
__m512d test_mm512_mask_max_pd (__m512d __W, __mmask8 __U, __m512d __A, __m512d __B) __m512d test_mm512_mask_max_pd (__m512d __W, __mmask8 __U, __m512d __A, __m512d __B)
{ {
// CHECK-LABEL: @test_mm512_mask_max_pd // CHECK-LABEL: @test_mm512_mask_max_pd
// CHECK: @llvm.x86.avx512.mask.max.pd.512 // CHECK: @llvm.x86.avx512.mask.max.pd.512
return _mm512_mask_max_pd (__W,__U,__A,__B); return _mm512_mask_max_pd (__W,__U,__A,__B);
} }
__m512d test_mm512_maskz_max_pd (__mmask8 __U, __m512d __A, __m512d __B) __m512d test_mm512_maskz_max_pd (__mmask8 __U, __m512d __A, __m512d __B)
▲ Show 20 Lines • Show All 95 Lines • ▼ Show 20 Lines
} }
__m512d test_mm512_maskz_roundscale_pd(__mmask8 __U, __m512d __A) __m512d test_mm512_maskz_roundscale_pd(__mmask8 __U, __m512d __A)
{ {
// CHECK-LABEL: @test_mm512_maskz_roundscale_pd // CHECK-LABEL: @test_mm512_maskz_roundscale_pd
// CHECK: @llvm.x86.avx512.mask.rndscale.pd.512 // CHECK: @llvm.x86.avx512.mask.rndscale.pd.512
return _mm512_maskz_roundscale_pd(__U,__A, 1); return _mm512_maskz_roundscale_pd(__U,__A, 1);
} }
__m512i test_mm512_mask_max_epi32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_max_epi32
// CHECK: @llvm.x86.avx512.mask.pmaxs.d.512
return _mm512_mask_max_epi32 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_max_epi32 (__mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_max_epi32
// CHECK: @llvm.x86.avx512.mask.pmaxs.d.512
return _mm512_maskz_max_epi32 (__M,__A,__B);
}
__m512i test_mm512_mask_max_epi64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_max_epi64
// CHECK: @llvm.x86.avx512.mask.pmaxs.q.512
return _mm512_mask_max_epi64 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_max_epi64 (__mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_max_epi64
// CHECK: @llvm.x86.avx512.mask.pmaxs.q.512
return _mm512_maskz_max_epi64 (__M,__A,__B);
}
__m512i test_mm512_mask_max_epu64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_max_epu64
// CHECK: @llvm.x86.avx512.mask.pmaxu.q.512
return _mm512_mask_max_epu64 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_max_epu64 (__mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_max_epu64
// CHECK: @llvm.x86.avx512.mask.pmaxu.q.512
return _mm512_maskz_max_epu64 (__M,__A,__B);
}
__m512i test_mm512_mask_max_epu32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_max_epu32
// CHECK: @llvm.x86.avx512.mask.pmaxu.d.512
return _mm512_mask_max_epu32 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_max_epu32 (__mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_max_epu32
// CHECK: @llvm.x86.avx512.mask.pmaxu.d.512
return _mm512_maskz_max_epu32 (__M,__A,__B);
}
__m512i test_mm512_mask_min_epi32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_min_epi32
// CHECK: @llvm.x86.avx512.mask.pmins.d.512
return _mm512_mask_min_epi32 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_min_epi32 (__mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_min_epi32
// CHECK: @llvm.x86.avx512.mask.pmins.d.512
return _mm512_maskz_min_epi32 (__M,__A,__B);
}
__m512i test_mm512_mask_min_epu32 (__m512i __W, __mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_min_epu32
// CHECK: @llvm.x86.avx512.mask.pminu.d.512
return _mm512_mask_min_epu32 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_min_epu32 (__mmask16 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_min_epu32
// CHECK: @llvm.x86.avx512.mask.pminu.d.512
return _mm512_maskz_min_epu32 (__M,__A,__B);
}
__m512i test_mm512_mask_min_epi64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_min_epi64
// CHECK: @llvm.x86.avx512.mask.pmins.q.512
return _mm512_mask_min_epi64 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_min_epi64 (__mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_min_epi64
// CHECK: @llvm.x86.avx512.mask.pmins.q.512
return _mm512_maskz_min_epi64 (__M,__A,__B);
}
__m512i test_mm512_mask_min_epu64 (__m512i __W, __mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_mask_min_epu64
// CHECK: @llvm.x86.avx512.mask.pminu.q.512
return _mm512_mask_min_epu64 (__W,__M,__A,__B);
}
__m512i test_mm512_maskz_min_epu64 (__mmask8 __M, __m512i __A, __m512i __B)
{
// CHECK-LABEL: @test_mm512_maskz_min_epu64
// CHECK: @llvm.x86.avx512.mask.pminu.q.512
return _mm512_maskz_min_epu64 (__M,__A,__B);
}