diff options
| author | Pengfei Wang <pengfei.wang@intel.com> | 2019-06-06 08:28:42 +0000 |
|---|---|---|
| committer | Pengfei Wang <pengfei.wang@intel.com> | 2019-06-06 08:28:42 +0000 |
| commit | 3a29f7c99c2f7b38f0611b7ff5af1fce608cebdd (patch) | |
| tree | 24db8342b75f11541705923ffcffe72299fd597d /clang/test | |
| parent | 3c82c57d2b50c6d7ac69e4d69c8914a02eeda0b7 (diff) | |
| download | bcm5719-llvm-3a29f7c99c2f7b38f0611b7ff5af1fce608cebdd.tar.gz bcm5719-llvm-3a29f7c99c2f7b38f0611b7ff5af1fce608cebdd.zip | |
[X86] Add ENQCMD instructions
For more details about these instructions, please refer to the latest
ISE document:
https://software.intel.com/en-us/download/intel-architecture-instruction-set-extensions-programming-reference.
Patch by Tianqing Wang (tianqing)
Differential Revision: https://reviews.llvm.org/D62282
llvm-svn: 362685
Diffstat (limited to 'clang/test')
| -rw-r--r-- | clang/test/CodeGen/x86-enqcmd-builtins.c | 20 | ||||
| -rw-r--r-- | clang/test/Driver/x86-target-features.c | 5 | ||||
| -rw-r--r-- | clang/test/Preprocessor/x86_target_features.c | 7 |
3 files changed, 32 insertions, 0 deletions
diff --git a/clang/test/CodeGen/x86-enqcmd-builtins.c b/clang/test/CodeGen/x86-enqcmd-builtins.c new file mode 100644 index 00000000000..e86e792718d --- /dev/null +++ b/clang/test/CodeGen/x86-enqcmd-builtins.c @@ -0,0 +1,20 @@ +// RUN: %clang_cc1 %s -ffreestanding -triple i386-unknown-unknown -target-feature +enqcmd -emit-llvm -o - | FileCheck %s +// RUN: %clang_cc1 %s -ffreestanding -triple x86_64-unknown-unknown -target-feature +enqcmd -emit-llvm -o - | FileCheck %s + +#include <immintrin.h> + +int test_enqcmd(void *dst, const void *src) { +// CHECK-LABEL: @test_enqcmd +// CHECK: %[[TMP0:.+]] = call i8 @llvm.x86.enqcmd(i8* %{{.+}}, i8* %{{.+}}) +// CHECK: %[[RET:.+]] = zext i8 %[[TMP0]] to i32 +// CHECK: ret i32 %[[RET]] + return _enqcmd(dst, src); +} + +int test_enqcmds(void *dst, const void *src) { +// CHECK-LABEL: @test_enqcmds +// CHECK: %[[TMP0:.+]] = call i8 @llvm.x86.enqcmds(i8* %{{.+}}, i8* %{{.+}}) +// CHECK: %[[RET:.+]] = zext i8 %[[TMP0]] to i32 +// CHECK: ret i32 %[[RET]] + return _enqcmds(dst, src); +} diff --git a/clang/test/Driver/x86-target-features.c b/clang/test/Driver/x86-target-features.c index 5866d38648e..ed9c0af1f96 100644 --- a/clang/test/Driver/x86-target-features.c +++ b/clang/test/Driver/x86-target-features.c @@ -188,3 +188,8 @@ // RUN: %clang -target i386-unknown-linux-gnu -march=i386 -mno-avx512bf16 %s -### -o %t.o 2>&1 | FileCheck -check-prefix=NO-AVX512BF16 %s // AVX512BF16: "-target-feature" "+avx512bf16" // NO-AVX512BF16: "-target-feature" "-avx512bf16" + +// RUN: %clang -target i386-unknown-linux-gnu -march=i386 -menqcmd %s -### -o %t.o 2>&1 | FileCheck --check-prefix=ENQCMD %s +// RUN: %clang -target i386-unknown-linux-gnu -march=i386 -mno-enqcmd %s -### -o %t.o 2>&1 | FileCheck --check-prefix=NO-ENQCMD %s +// ENQCMD: "-target-feature" "+enqcmd" +// NO-ENQCMD: "-target-feature" "-enqcmd" diff --git a/clang/test/Preprocessor/x86_target_features.c b/clang/test/Preprocessor/x86_target_features.c index 2dfca34121c..290ce3bf1dc 100644 --- a/clang/test/Preprocessor/x86_target_features.c +++ b/clang/test/Preprocessor/x86_target_features.c @@ -468,3 +468,10 @@ // NOVP2INTERSECT-NOT: #define __AVX512VP2INTERSECT__ 1 +// RUN: %clang -target i386-unknown-unknown -march=atom -menqcmd -x c -E -dM -o - %s | FileCheck -match-full-lines --check-prefix=ENQCMD %s + +// ENQCMD: #define __ENQCMD__ 1 + +// RUN: %clang -target i386-unknown-unknown -march=atom -mno-enqcmd -x c -E -dM -o - %s | FileCheck -match-full-lines --check-prefix=NOENQCMD %s + +// NOENQCMD-NOT: #define __ENQCMD__ 1 |
