c7fb0eed05
ADC and ADX use the same internal intrinsics - for testing I've taken the same approach as the generic builtin overflow tests, putting the intrinsics in a constexpr test wrapper and comparing the carry/result value pair. I've added the addcarry/subborrow intrinsics to the clang language extension list - I'm not sure if we want to add all ISA intrinsics to the list (although we can if people think it useful?), but I felt we should at least include the baseline x86 intrinsics.
69 lines
3.2 KiB
C
69 lines
3.2 KiB
C
// RUN: %clang_cc1 -x c -triple x86_64-unknown-unknown -ffreestanding -target-feature +adx -emit-llvm -o - %s | FileCheck %s
|
|
// RUN: %clang_cc1 -x c++ -triple x86_64-unknown-unknown -ffreestanding -target-feature +adx -emit-llvm -o - %s | FileCheck %s
|
|
|
|
#include <immintrin.h>
|
|
|
|
unsigned char test_addcarryx_u32(unsigned char __cf, unsigned int __x,
|
|
unsigned int __y, unsigned int *__p) {
|
|
// CHECK-LABEL: test_addcarryx_u32
|
|
// CHECK: [[ADC:%.*]] = call { i8, i32 } @llvm.x86.addcarry.32
|
|
// CHECK: [[DATA:%.*]] = extractvalue { i8, i32 } [[ADC]], 1
|
|
// CHECK: store i32 [[DATA]], ptr %{{.*}}
|
|
// CHECK: [[CF:%.*]] = extractvalue { i8, i32 } [[ADC]], 0
|
|
return _addcarryx_u32(__cf, __x, __y, __p);
|
|
}
|
|
|
|
unsigned char test_addcarryx_u64(unsigned char __cf, unsigned long long __x,
|
|
unsigned long long __y,
|
|
unsigned long long *__p) {
|
|
// CHECK-LABEL: test_addcarryx_u64
|
|
// CHECK: [[ADC:%.*]] = call { i8, i64 } @llvm.x86.addcarry.64
|
|
// CHECK: [[DATA:%.*]] = extractvalue { i8, i64 } [[ADC]], 1
|
|
// CHECK: store i64 [[DATA]], ptr %{{.*}}
|
|
// CHECK: [[CF:%.*]] = extractvalue { i8, i64 } [[ADC]], 0
|
|
return _addcarryx_u64(__cf, __x, __y, __p);
|
|
}
|
|
|
|
// Test constexpr handling.
|
|
#if defined(__cplusplus) && (__cplusplus >= 201103L)
|
|
|
|
template<typename X>
|
|
struct Result {
|
|
unsigned char A;
|
|
X B;
|
|
constexpr bool operator==(const Result<X> &Other) {
|
|
return A == Other.A && B == Other.B;
|
|
}
|
|
};
|
|
|
|
constexpr Result<unsigned int>
|
|
const_test_addcarryx_u32(unsigned char __cf, unsigned int __x, unsigned int __y)
|
|
{
|
|
unsigned int __r{};
|
|
return { _addcarryx_u32(__cf, __x, __y, &__r), __r };
|
|
}
|
|
|
|
void constexpr addxu32() {
|
|
static_assert(const_test_addcarryx_u32(0, 0x00000000, 0x00000000) == Result<unsigned int>{0, 0x00000000});
|
|
static_assert(const_test_addcarryx_u32(1, 0xFFFFFFFE, 0x00000000) == Result<unsigned int>{0, 0xFFFFFFFF});
|
|
static_assert(const_test_addcarryx_u32(1, 0xFFFFFFFE, 0x00000001) == Result<unsigned int>{1, 0x00000000});
|
|
static_assert(const_test_addcarryx_u32(0, 0xFFFFFFFF, 0xFFFFFFFF) == Result<unsigned int>{1, 0xFFFFFFFE});
|
|
static_assert(const_test_addcarryx_u32(1, 0xFFFFFFFF, 0xFFFFFFFF) == Result<unsigned int>{1, 0xFFFFFFFF});
|
|
}
|
|
|
|
constexpr Result<unsigned long long>
|
|
const_test_addcarryx_u64(unsigned char __cf, unsigned long long __x, unsigned long long __y)
|
|
{
|
|
unsigned long long __r{};
|
|
return { _addcarryx_u64(__cf, __x, __y, &__r), __r };
|
|
}
|
|
|
|
void constexpr addxu64() {
|
|
static_assert(const_test_addcarryx_u64(0, 0x0000000000000000ULL, 0x0000000000000000ULL) == Result<unsigned long long>{0, 0x0000000000000000ULL});
|
|
static_assert(const_test_addcarryx_u64(1, 0xFFFFFFFFFFFFFFFEULL, 0x0000000000000000ULL) == Result<unsigned long long>{0, 0xFFFFFFFFFFFFFFFFULL});
|
|
static_assert(const_test_addcarryx_u64(1, 0xFFFFFFFFFFFFFFFEULL, 0x0000000000000001ULL) == Result<unsigned long long>{1, 0x0000000000000000ULL});
|
|
static_assert(const_test_addcarryx_u64(0, 0xFFFFFFFFFFFFFFFFULL, 0xFFFFFFFFFFFFFFFFULL) == Result<unsigned long long>{1, 0xFFFFFFFFFFFFFFFEULL});
|
|
static_assert(const_test_addcarryx_u64(1, 0xFFFFFFFFFFFFFFFFULL, 0xFFFFFFFFFFFFFFFFULL) == Result<unsigned long long>{1, 0xFFFFFFFFFFFFFFFFULL});
|
|
}
|
|
|
|
#endif |