This is an archive of the discontinued LLVM Phabricator instance.

Differential D20070

[Clang][AVX512] completing missing intrinsics [roundscale, ceil, floor]
ClosedPublic

Authored by m_zuckerman on May 9 2016, 8:35 AM.

Details

Reviewers
AsafBadouh
delena
igorb
Commits
rG7360d8a9cc77: [Clang][AVX512] completing missing intrinsics [roundscale, ceil, floor]
rC269022: [Clang][AVX512] completing missing intrinsics [roundscale, ceil, floor]
rL269022: [Clang][AVX512] completing missing intrinsics [roundscale, ceil, floor]

Diff Detail

Event Timeline

m_zuckerman updated this revision to Diff 56583.May 9 2016, 8:35 AM
m_zuckerman retitled this revision from to [Clang][AVX512] completing missing intrinsics [roundscale, ceil, floor].
m_zuckerman updated this object.
m_zuckerman added reviewers: AsafBadouh, igorb, delena.
delena accepted this revision.May 9 2016, 12:18 PM
delena edited edge metadata.
This revision is now accepted and ready to land.May 9 2016, 12:18 PM
Closed by commit rL269022: [Clang][AVX512] completing missing intrinsics [roundscale, ceil, floor] (authored by mzuckerm). · Explain WhyMay 10 2016, 12:37 AM
This revision was automatically updated to reflect the committed changes.

Revision Contents

PathSize
lib/
Headers/
avx512fintrin.h
avx512fintrin.h (revision 268910)
62 lines
test/
CodeGen/
avx512f-builtins.c
avx512f-builtins.c (revision 268910)
54 lines

Diff 56583

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,301 Lines • ▼ Show 20 Lines
_mm512_floor_ps(__m512 __A) _mm512_floor_ps(__m512 __A)
{ {
return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A, return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A,
_MM_FROUND_FLOOR, _MM_FROUND_FLOOR,
(__v16sf) __A, -1, (__v16sf) __A, -1,
_MM_FROUND_CUR_DIRECTION); _MM_FROUND_CUR_DIRECTION);
} }
static __inline__ __m512 __DEFAULT_FN_ATTRS
_mm512_mask_floor_ps (__m512 __W, __mmask16 __U, __m512 __A)
{
return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A,
_MM_FROUND_FLOOR,
(__v16sf) __W, __U,
_MM_FROUND_CUR_DIRECTION);
}
static __inline __m512d __DEFAULT_FN_ATTRS static __inline __m512d __DEFAULT_FN_ATTRS
_mm512_floor_pd(__m512d __A) _mm512_floor_pd(__m512d __A)
{ {
return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A, return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A,
_MM_FROUND_FLOOR, _MM_FROUND_FLOOR,
(__v8df) __A, -1, (__v8df) __A, -1,
_MM_FROUND_CUR_DIRECTION); _MM_FROUND_CUR_DIRECTION);
} }
static __inline__ __m512d __DEFAULT_FN_ATTRS
_mm512_mask_floor_pd (__m512d __W, __mmask8 __U, __m512d __A)
{
return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A,
_MM_FROUND_FLOOR,
(__v8df) __W, __U,
_MM_FROUND_CUR_DIRECTION);
}
static __inline__ __m512 __DEFAULT_FN_ATTRS
_mm512_mask_ceil_ps (__m512 __W, __mmask16 __U, __m512 __A)
{
return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A,
_MM_FROUND_CEIL,
(__v16sf) __W, __U,
_MM_FROUND_CUR_DIRECTION);
}
static __inline __m512 __DEFAULT_FN_ATTRS static __inline __m512 __DEFAULT_FN_ATTRS
_mm512_ceil_ps(__m512 __A) _mm512_ceil_ps(__m512 __A)
{ {
return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A, return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A,
_MM_FROUND_CEIL, _MM_FROUND_CEIL,
(__v16sf) __A, -1, (__v16sf) __A, -1,
_MM_FROUND_CUR_DIRECTION); _MM_FROUND_CUR_DIRECTION);
} }
static __inline __m512d __DEFAULT_FN_ATTRS static __inline __m512d __DEFAULT_FN_ATTRS
_mm512_ceil_pd(__m512d __A) _mm512_ceil_pd(__m512d __A)
{ {
return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A, return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A,
_MM_FROUND_CEIL, _MM_FROUND_CEIL,
(__v8df) __A, -1, (__v8df) __A, -1,
_MM_FROUND_CUR_DIRECTION); _MM_FROUND_CUR_DIRECTION);
} }
static __inline__ __m512d __DEFAULT_FN_ATTRS
_mm512_mask_ceil_pd (__m512d __W, __mmask8 __U, __m512d __A)
{
return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A,
_MM_FROUND_CEIL,
(__v8df) __W, __U,
_MM_FROUND_CUR_DIRECTION);
}
static __inline __m512i __DEFAULT_FN_ATTRS static __inline __m512i __DEFAULT_FN_ATTRS
_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);
} }
▲ Show 20 Lines • Show All 489 Lines • ▼ Show 20 Lines
#define _mm512_maskz_div_round_ps(__U, __A, __B, __R) __extension__ ({ \ #define _mm512_maskz_div_round_ps(__U, __A, __B, __R) __extension__ ({ \
(__m512) __builtin_ia32_divps512_mask ((__v16sf) __A, (__v16sf) __B, \ (__m512) __builtin_ia32_divps512_mask ((__v16sf) __A, (__v16sf) __B, \
(__v16sf) _mm512_setzero_ps (), (__mmask16) __U, __R);}); (__v16sf) _mm512_setzero_ps (), (__mmask16) __U, __R);});
#define _mm512_roundscale_ps(A, B) __extension__ ({ \ #define _mm512_roundscale_ps(A, B) __extension__ ({ \
(__m512)__builtin_ia32_rndscaleps_mask((__v16sf)(A), (B), (__v16sf)(A), \ (__m512)__builtin_ia32_rndscaleps_mask((__v16sf)(A), (B), (__v16sf)(A), \
-1, _MM_FROUND_CUR_DIRECTION); }) -1, _MM_FROUND_CUR_DIRECTION); })
#define _mm512_mask_roundscale_ps( __A, __B, __C, __imm) __extension__ ({\
(__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __C, __imm,\
(__v16sf) __A,(__mmask16) __B,\
_MM_FROUND_CUR_DIRECTION);\
})
#define _mm512_maskz_roundscale_ps( __A, __B, __imm) __extension__ ({\
(__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __B, __imm,\
(__v16sf) _mm512_setzero_ps (),\
(__mmask16) __A, _MM_FROUND_CUR_DIRECTION);\
})
#define _mm512_roundscale_pd(A, B) __extension__ ({ \ #define _mm512_roundscale_pd(A, B) __extension__ ({ \
(__m512d)__builtin_ia32_rndscalepd_mask((__v8df)(A), (B), (__v8df)(A), \ (__m512d)__builtin_ia32_rndscalepd_mask((__v8df)(A), (B), (__v8df)(A), \
-1, _MM_FROUND_CUR_DIRECTION); }) -1, _MM_FROUND_CUR_DIRECTION); })
#define _mm512_mask_roundscale_pd(__A, __B, __C, __imm) __extension__ ({\
(__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __C, __imm,\
(__v8df) __A, (__mmask8) __B,\
_MM_FROUND_CUR_DIRECTION);\
})
#define _mm512_maskz_roundscale_pd(__A, __B, __imm) __extension__ ({\
(__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __B, __imm,\
(__v8df) _mm512_setzero_pd (),\
(__mmask8) __A, _MM_FROUND_CUR_DIRECTION);\
})
#define _mm512_fmadd_round_pd(A, B, C, R) __extension__ ({ \ #define _mm512_fmadd_round_pd(A, B, C, R) __extension__ ({ \
(__m512d) __builtin_ia32_vfmaddpd512_mask ((__v8df) (A), \ (__m512d) __builtin_ia32_vfmaddpd512_mask ((__v8df) (A), \
(__v8df) (B), (__v8df) (C), \ (__v8df) (B), (__v8df) (C), \
(__mmask8) -1, (R)); }) (__mmask8) -1, (R)); })
#define _mm512_mask_fmadd_round_pd(A, U, B, C, R) __extension__ ({ \ #define _mm512_mask_fmadd_round_pd(A, U, B, C, R) __extension__ ({ \
(__m512d) __builtin_ia32_vfmaddpd512_mask ((__v8df) (A), \ (__m512d) __builtin_ia32_vfmaddpd512_mask ((__v8df) (A), \
▲ Show 20 Lines • Show All 6,718 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);
} }
__m512 test_mm512_mask_floor_ps (__m512 __W, __mmask16 __U, __m512 __A)
{
// CHECK-LABEL: @test_mm512_mask_floor_ps
// CHECK: @llvm.x86.avx512.mask.rndscale.ps.512
return _mm512_mask_floor_ps (__W,__U,__A);
}
__m512d test_mm512_mask_floor_pd (__m512d __W, __mmask8 __U, __m512d __A)
{
// CHECK-LABEL: @test_mm512_mask_floor_pd
// CHECK: @llvm.x86.avx512.mask.rndscale.pd.512
return _mm512_mask_floor_pd (__W,__U,__A);
}
__m512 test_mm512_mask_ceil_ps (__m512 __W, __mmask16 __U, __m512 __A)
{
// CHECK-LABEL: @test_mm512_mask_ceil_ps
// CHECK: @llvm.x86.avx512.mask.rndscale.ps.512
return _mm512_mask_ceil_ps (__W,__U,__A);
}
__m512d test_mm512_mask_ceil_pd (__m512d __W, __mmask8 __U, __m512d __A)
{
// CHECK-LABEL: @test_mm512_mask_ceil_pd
// CHECK: @llvm.x86.avx512.mask.rndscale.pd.512
return _mm512_mask_ceil_pd (__W,__U,__A);
}
__m512 test_mm512_mask_roundscale_ps(__m512d __W, __mmask8 __U, __m512d __A)
{
// CHECK-LABEL: @test_mm512_mask_roundscale_ps
// CHECK: @llvm.x86.avx512.mask.rndscale.ps.512
return _mm512_mask_roundscale_ps(__W,__U,__A, 1);
}
__m512 test_mm512_maskz_roundscale_ps(__mmask8 __U, __m512d __A)
{
// CHECK-LABEL: @test_mm512_maskz_roundscale_ps
// CHECK: @llvm.x86.avx512.mask.rndscale.ps.512
return _mm512_maskz_roundscale_ps(__U,__A, 1);
}
__m512d test_mm512_mask_roundscale_pd(__m512d __W, __mmask8 __U, __m512d __A)
{
// CHECK-LABEL: @test_mm512_mask_roundscale_pd
// CHECK: @llvm.x86.avx512.mask.rndscale.pd.512
return _mm512_mask_roundscale_pd(__W,__U,__A, 1);
}
__m512d test_mm512_maskz_roundscale_pd(__mmask8 __U, __m512d __A)
{
// CHECK-LABEL: @test_mm512_maskz_roundscale_pd
// CHECK: @llvm.x86.avx512.mask.rndscale.pd.512
return _mm512_maskz_roundscale_pd(__U,__A, 1);
}