blob: c79819b75f60d087dadcfacce7512f0c1fc1feae (
plain)
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
|
#include<simdconfig.h>
#include<simdfuncs.h>
#include<stdint.h>
/*
* FIXME add proper runtime detection for VS.
*/
#ifdef _MSC_VER
#include<intrin.h>
int avx2_available(void) {
return 0;
}
#else
#include<immintrin.h>
#include<cpuid.h>
#if defined(__APPLE__)
int avx2_available(void) { return 0; }
#else
int avx2_available(void) {
return __builtin_cpu_supports("avx2");
}
#endif
#endif
void increment_avx2(float arr[4]) {
double darr[4];
darr[0] = arr[0];
darr[1] = arr[1];
darr[2] = arr[2];
darr[3] = arr[3];
__m256d val = _mm256_loadu_pd(darr);
__m256d one = _mm256_set1_pd(1.0);
__m256d result = _mm256_add_pd(val, one);
_mm256_storeu_pd(darr, result);
one = _mm256_permute4x64_pd(one, 66); /* A no-op, just here to use AVX2. */
arr[0] = (float)darr[0];
arr[1] = (float)darr[1];
arr[2] = (float)darr[2];
arr[3] = (float)darr[3];
}
|
