This is an archive of the discontinued LLVM Phabricator instance.

Differential D17919

[CLANG][AVX512][BUILTIN] Add builtin vcomi{ss|sd}
ClosedPublic

Authored by m_zuckerman on Mar 6 2016, 8:02 AM.

Details

Reviewers
AsafBadouh
delena
igorb
Commits
rGe71d59fc4f91: [CLANG][AVX512][BUILTIN] Add builtin vcomi{ss|sd}
rC262847: [CLANG][AVX512][BUILTIN] Add builtin vcomi{ss|sd}
rL262847: [CLANG][AVX512][BUILTIN] Add builtin vcomi{ss|sd}

Diff Detail

Repository
rL LLVM

Event Timeline

m_zuckerman updated this revision to Diff 49919.Mar 6 2016, 8:02 AM
m_zuckerman retitled this revision from to [CLANG][AVX512][BUILTIN] Add builtin vcomi{ss|sd} .
m_zuckerman updated this object.
m_zuckerman added reviewers: AsafBadouh, igorb, delena.
m_zuckerman added a subscriber: llvm-commits.
delena accepted this revision.Mar 6 2016, 9:07 AM
delena edited edge metadata.

LGTM

This revision is now accepted and ready to land.Mar 6 2016, 9:07 AM
Closed by commit rL262847: [CLANG][AVX512][BUILTIN] Add builtin vcomi{ss|sd} (authored by mzuckerm). · Explain WhyMar 7 2016, 11:19 AM
This revision was automatically updated to reflect the committed changes.

Revision Contents

PathSize
cfe/
trunk/
include/
clang/
Basic/
2 lines
lib/
Headers/
8 lines
test/
CodeGen/
10 lines

Diff 49983

cfe/trunk/include/clang/Basic/BuiltinsX86.def

Show First 20 Lines • Show All 1,741 Lines • ▼ Show 20 Lines
TARGET_BUILTIN(__builtin_ia32_vpermt2varqi512_mask, "V64cV64cV64cV64cULLi","","avx512vbmi") TARGET_BUILTIN(__builtin_ia32_vpermt2varqi512_mask, "V64cV64cV64cV64cULLi","","avx512vbmi")
TARGET_BUILTIN(__builtin_ia32_vpermt2varqi512_maskz, "V64cV64cV64cV64cULLi","","avx512vbmi") TARGET_BUILTIN(__builtin_ia32_vpermt2varqi512_maskz, "V64cV64cV64cV64cULLi","","avx512vbmi")
TARGET_BUILTIN(__builtin_ia32_vpermi2varqi128_mask, "V16cV16cV16cV16cUs","","avx512vbmi,avx512vl") TARGET_BUILTIN(__builtin_ia32_vpermi2varqi128_mask, "V16cV16cV16cV16cUs","","avx512vbmi,avx512vl")
TARGET_BUILTIN(__builtin_ia32_vpermi2varqi256_mask, "V32cV32cV32cV32cUi","","avx512vbmi,avx512vl") TARGET_BUILTIN(__builtin_ia32_vpermi2varqi256_mask, "V32cV32cV32cV32cUi","","avx512vbmi,avx512vl")
TARGET_BUILTIN(__builtin_ia32_vpermt2varqi128_mask, "V16cV16cV16cV16cUs","","avx512vbmi,avx512vl") TARGET_BUILTIN(__builtin_ia32_vpermt2varqi128_mask, "V16cV16cV16cV16cUs","","avx512vbmi,avx512vl")
TARGET_BUILTIN(__builtin_ia32_vpermt2varqi128_maskz, "V16cV16cV16cV16cUs","","avx512vbmi,avx512vl") TARGET_BUILTIN(__builtin_ia32_vpermt2varqi128_maskz, "V16cV16cV16cV16cUs","","avx512vbmi,avx512vl")
TARGET_BUILTIN(__builtin_ia32_vpermt2varqi256_mask, "V32cV32cV32cV32cUi","","avx512vbmi,avx512vl") TARGET_BUILTIN(__builtin_ia32_vpermt2varqi256_mask, "V32cV32cV32cV32cUi","","avx512vbmi,avx512vl")
TARGET_BUILTIN(__builtin_ia32_vpermt2varqi256_maskz, "V32cV32cV32cV32cUi","","avx512vbmi,avx512vl") TARGET_BUILTIN(__builtin_ia32_vpermt2varqi256_maskz, "V32cV32cV32cV32cUi","","avx512vbmi,avx512vl")
TARGET_BUILTIN(__builtin_ia32_vcomisd, "iV2dV2dIiIi","","avx512f")
TARGET_BUILTIN(__builtin_ia32_vcomiss, "iV4fV4fIiIi","","avx512f")
#undef BUILTIN #undef BUILTIN
#undef TARGET_BUILTIN #undef TARGET_BUILTIN

cfe/trunk/lib/Headers/avx512fintrin.h

Show First 20 Lines • Show All 3,689 Lines • ▼ Show 20 Lines
_mm512_maskz_movedup_pd (__mmask8 __U, __m512d __A) _mm512_maskz_movedup_pd (__mmask8 __U, __m512d __A)
{ {
return (__m512d) __builtin_ia32_movddup512_mask ((__v8df) __A, return (__m512d) __builtin_ia32_movddup512_mask ((__v8df) __A,
(__v8df) (__v8df)
_mm512_setzero_pd (), _mm512_setzero_pd (),
(__mmask8) __U); (__mmask8) __U);
} }
#define _mm_comi_round_sd(__A, __B, __P, __R) __extension__ ({\
__builtin_ia32_vcomisd ((__v2df) (__A), (__v2df) (__B), ( __P), ( __R));\
})
#define _mm_comi_round_ss( __A, __B, __P, __R) __extension__ ({\
__builtin_ia32_vcomiss ((__v4sf) (__A), (__v4sf) (__B), ( __P), ( __R));\
})
#undef __DEFAULT_FN_ATTRS #undef __DEFAULT_FN_ATTRS
#endif // __AVX512FINTRIN_H #endif // __AVX512FINTRIN_H

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

Show First 20 Lines • Show All 2,358 Lines • ▼ Show 20 Lines
} }
__m512d test_mm512_maskz_movedup_pd(__mmask8 __U, __m512d __A) { __m512d test_mm512_maskz_movedup_pd(__mmask8 __U, __m512d __A) {
// CHECK-LABEL: @test_mm512_maskz_movedup_pd // CHECK-LABEL: @test_mm512_maskz_movedup_pd
// CHECK: @llvm.x86.avx512.mask.movddup.512 // CHECK: @llvm.x86.avx512.mask.movddup.512
return _mm512_maskz_movedup_pd(__U, __A); return _mm512_maskz_movedup_pd(__U, __A);
} }
int test_mm_comi_round_sd(__m128d __A, __m128d __B) {
// CHECK-LABEL: @test_mm_comi_round_sd
// CHECK: @llvm.x86.avx512.vcomi.sd
return _mm_comi_round_sd(__A, __B, 5, 3);
}
int test_mm_comi_round_ss(__m128 __A, __m128 __B) {
// CHECK-LABEL: @test_mm_comi_round_ss
// CHECK: @llvm.x86.avx512.vcomi.ss
return _mm_comi_round_ss(__A, __B, 5, 3);
}