| Gabor Buella | a51e0c2 | 2018-05-01 10:05:42 +0000 | [diff] [blame] | 1 | // RUN: %clang_cc1 -ffreestanding -Wall -pedantic -triple x86_64-unknown-unknown -target-feature +movdiri -target-feature +movdir64b %s -emit-llvm -o - | FileCheck %s --check-prefix=X86_64 --check-prefix=CHECK |
| Gabor Buella | 9cd4f16 | 2018-05-11 14:22:04 +0000 | [diff] [blame] | 2 | // RUN: %clang_cc1 -ffreestanding -Wall -pedantic -triple i386-unknown-unknown -target-feature +movdiri -target-feature +movdir64b %s -emit-llvm -o - | FileCheck %s --check-prefix=X86 --check-prefix=CHECK |
| Gabor Buella | a51e0c2 | 2018-05-01 10:05:42 +0000 | [diff] [blame] | 3 | |
| Gabor Buella | 5219ed8 | 2018-05-24 07:09:08 +0000 | [diff] [blame] | 4 | #include <immintrin.h> |
| Gabor Buella | a51e0c2 | 2018-05-01 10:05:42 +0000 | [diff] [blame] | 5 | #include <stdint.h> |
| 6 | |
| 7 | void test_directstore32(void *dst, uint32_t value) { |
| 8 | // CHECK-LABEL: test_directstore32 |
| 9 | // CHECK: call void @llvm.x86.directstore32 |
| 10 | _directstoreu_u32(dst, value); |
| 11 | } |
| 12 | |
| 13 | #ifdef __x86_64__ |
| 14 | |
| 15 | void test_directstore64(void *dst, uint64_t value) { |
| 16 | // X86_64-LABEL: test_directstore64 |
| 17 | // X86_64: call void @llvm.x86.directstore64 |
| 18 | _directstoreu_u64(dst, value); |
| 19 | } |
| 20 | |
| 21 | #endif |
| 22 | |
| 23 | void test_dir64b(void *dst, const void *src) { |
| 24 | // CHECK-LABEL: test_dir64b |
| Gabor Buella | 9cd4f16 | 2018-05-11 14:22:04 +0000 | [diff] [blame] | 25 | // CHECK: [[PTRINT1:%.+]] = ptrtoint |
| 26 | // X86: [[MASKEDPTR1:%.+]] = and i32 [[PTRINT1]], 63 |
| 27 | // X86: [[MASKCOND1:%.+]] = icmp eq i32 [[MASKEDPTR1]], 0 |
| 28 | // X86_64: [[MASKEDPTR1:%.+]] = and i64 [[PTRINT1]], 63 |
| 29 | // X86_64: [[MASKCOND1:%.+]] = icmp eq i64 [[MASKEDPTR1]], 0 |
| Gabor Buella | a51e0c2 | 2018-05-01 10:05:42 +0000 | [diff] [blame] | 30 | // CHECK: call void @llvm.x86.movdir64b |
| 31 | _movdir64b(dst, src); |
| 32 | } |
| 33 | |
| 34 | // CHECK: declare void @llvm.x86.directstore32(i8*, i32) |
| 35 | // X86_64: declare void @llvm.x86.directstore64(i8*, i64) |
| 36 | // CHECK: declare void @llvm.x86.movdir64b(i8*, i8*) |