minix/external/bsd/llvm/dist/clang/test/CodeGen/avx-builtins.c
Lionel Sambuc f4a2713ac8 Importing netbsd clang -- pristine
Change-Id: Ia40e9ffdf29b5dab2f122f673ff6802a58bc690f
2014-07-28 17:05:57 +02:00

113 lines
2.9 KiB
C

// RUN: %clang_cc1 %s -O3 -triple=x86_64-apple-darwin -target-feature +avx -emit-llvm -o - | FileCheck %s
// Don't include mm_malloc.h, it's system specific.
#define __MM_MALLOC_H
#include <immintrin.h>
//
// Test LLVM IR codegen of shuffle instructions
//
__m256 test__mm256_loadu_ps(void* p) {
// CHECK: load <8 x float>* %{{.*}}, align 1
return _mm256_loadu_ps(p);
}
__m256d test__mm256_loadu_pd(void* p) {
// CHECK: load <4 x double>* %{{.*}}, align 1
return _mm256_loadu_pd(p);
}
__m256i test__mm256_loadu_si256(void* p) {
// CHECK: load <4 x i64>* %{{.+}}, align 1
return _mm256_loadu_si256(p);
}
__m128i test_mm_cmpestrm(__m128i A, int LA, __m128i B, int LB) {
// CHECK: @llvm.x86.sse42.pcmpestrm128
return _mm_cmpestrm(A, LA, B, LB, 7);
}
int test_mm_cmpestri(__m128i A, int LA, __m128i B, int LB) {
// CHECK: @llvm.x86.sse42.pcmpestri128
return _mm_cmpestri(A, LA, B, LB, 7);
}
int test_mm_cmpestra(__m128i A, int LA, __m128i B, int LB) {
// CHECK: @llvm.x86.sse42.pcmpestria128
return _mm_cmpestra(A, LA, B, LB, 7);
}
int test_mm_cmpestrc(__m128i A, int LA, __m128i B, int LB) {
// CHECK: @llvm.x86.sse42.pcmpestric128
return _mm_cmpestrc(A, LA, B, LB, 7);
}
int test_mm_cmpestro(__m128i A, int LA, __m128i B, int LB) {
// CHECK: @llvm.x86.sse42.pcmpestrio128
return _mm_cmpestro(A, LA, B, LB, 7);
}
int test_mm_cmpestrs(__m128i A, int LA, __m128i B, int LB) {
// CHECK: @llvm.x86.sse42.pcmpestris128
return _mm_cmpestrs(A, LA, B, LB, 7);
}
int test_mm_cmpestrz(__m128i A, int LA, __m128i B, int LB) {
// CHECK: @llvm.x86.sse42.pcmpestriz128
return _mm_cmpestrz(A, LA, B, LB, 7);
}
__m128i test_mm_cmpistrm(__m128i A, __m128i B) {
// CHECK: @llvm.x86.sse42.pcmpistrm128
return _mm_cmpistrm(A, B, 7);
}
int test_mm_cmpistri(__m128i A, __m128i B) {
// CHECK: @llvm.x86.sse42.pcmpistri128
return _mm_cmpistri(A, B, 7);
}
int test_mm_cmpistra(__m128i A, __m128i B) {
// CHECK: @llvm.x86.sse42.pcmpistria128
return _mm_cmpistra(A, B, 7);
}
int test_mm_cmpistrc(__m128i A, __m128i B) {
// CHECK: @llvm.x86.sse42.pcmpistric128
return _mm_cmpistrc(A, B, 7);
}
int test_mm_cmpistro(__m128i A, __m128i B) {
// CHECK: @llvm.x86.sse42.pcmpistrio128
return _mm_cmpistro(A, B, 7);
}
int test_mm_cmpistrs(__m128i A, __m128i B) {
// CHECK: @llvm.x86.sse42.pcmpistris128
return _mm_cmpistrs(A, B, 7);
}
int test_mm_cmpistrz(__m128i A, __m128i B) {
// CHECK: @llvm.x86.sse42.pcmpistriz128
return _mm_cmpistrz(A, B, 7);
}
int test_extract_epi32(__m256i __a) {
// CHECK-LABEL: @test_extract_epi32
// CHECK: extractelement <8 x i32> %{{.*}}, i32 0
return _mm256_extract_epi32(__a, 8);
}
int test_extract_epi16(__m256i __a) {
// CHECK-LABEL: @test_extract_epi16
// CHECK: extractelement <16 x i16> %{{.*}}, i32 0
return _mm256_extract_epi16(__a, 16);
}
int test_extract_epi8(__m256i __a) {
// CHECK-LABEL: @test_extract_epi8
// CHECK: extractelement <32 x i8> %{{.*}}, i32 0
return _mm256_extract_epi8(__a, 32);
}