aboutsummaryrefslogtreecommitdiff
diff options
context:
space:
mode:
authorJussi Pakkanen <jpakkane@gmail.com>2017-02-12 15:27:17 +0200
committerJussi Pakkanen <jpakkane@gmail.com>2017-07-17 19:00:42 +0300
commit9e5578ac472287979898f9ee8da72cccdf347636 (patch)
tree7bf139aa030c91c10e3cd1071d440fe1a7be2459
parent4a8ca14d44a4a6f67da0466dc98c81b3e5872194 (diff)
downloadmeson-9e5578ac472287979898f9ee8da72cccdf347636.zip
meson-9e5578ac472287979898f9ee8da72cccdf347636.tar.gz
meson-9e5578ac472287979898f9ee8da72cccdf347636.tar.bz2
Added SSE support.
-rw-r--r--test cases/common/139 simd/meson.build16
-rw-r--r--test cases/common/139 simd/simd_mmx.c3
-rw-r--r--test cases/common/139 simd/simd_sse.c17
-rw-r--r--test cases/common/139 simd/simdchecker.c16
4 files changed, 47 insertions, 5 deletions
diff --git a/test cases/common/139 simd/meson.build b/test cases/common/139 simd/meson.build
index 153b458..5311460 100644
--- a/test cases/common/139 simd/meson.build
+++ b/test cases/common/139 simd/meson.build
@@ -16,6 +16,17 @@ cdata = configuration_data()
#
# and then have a target that uses the result in links_with.
+# The following headers need to be added. Also Thumb and Altivec.
+#<emmintrin.h> SSE2
+#<pmmintrin.h> SSE3
+#<tmmintrin.h> SSSE3
+#<smmintrin.h> SSE4.1
+#<nmmintrin.h> SSE4.2
+#<ammintrin.h> SSE4A
+#<wmmintrin.h> AES
+#<immintrin.h> AVX
+#<zmmintrin.h> AVX512
+
simdlibs = []
if cc.has_argument('-mmmx')
@@ -23,6 +34,11 @@ if cc.has_argument('-mmmx')
simdlibs += static_library('simd_mmx', 'simd_mmx.c', c_args : '-mmmx')
endif
+if cc.has_argument('-msse')
+ cdata.set('HAVE_SSE', 1)
+ simdlibs += static_library('simd_sse', 'simd_sse.c', c_args : '-msse')
+endif
+
configure_file(output : 'simdconfig.h',
configuration : cdata)
diff --git a/test cases/common/139 simd/simd_mmx.c b/test cases/common/139 simd/simd_mmx.c
index dc1d51c..351f36e 100644
--- a/test cases/common/139 simd/simd_mmx.c
+++ b/test cases/common/139 simd/simd_mmx.c
@@ -1,3 +1,6 @@
+#include<simdconfig.h>
+#include<simdfuncs.h>
+
#include<mmintrin.h>
#include<cpuid.h>
#include<stdint.h>
diff --git a/test cases/common/139 simd/simd_sse.c b/test cases/common/139 simd/simd_sse.c
new file mode 100644
index 0000000..11a74c9
--- /dev/null
+++ b/test cases/common/139 simd/simd_sse.c
@@ -0,0 +1,17 @@
+#include<simdconfig.h>
+#include<simdfuncs.h>
+
+#include<xmmintrin.h>
+#include<cpuid.h>
+#include<stdint.h>
+
+int sse_available() {
+ return __builtin_cpu_supports("sse");
+}
+
+void increment_sse(float arr[4]) {
+ __m128 val = _mm_load_ps(arr);
+ __m128 one = _mm_set_ps1(1.0);
+ __m128 result = _mm_add_ps(val, one);
+ _mm_storeu_ps(arr, result);
+}
diff --git a/test cases/common/139 simd/simdchecker.c b/test cases/common/139 simd/simdchecker.c
index d75af25..b3c94f9 100644
--- a/test cases/common/139 simd/simdchecker.c
+++ b/test cases/common/139 simd/simdchecker.c
@@ -12,12 +12,18 @@ int main(int argc, char **argv) {
const float expected[4] = {3.0, 4.0, 5.0, 6.0};
void (*fptr)(float[4]) = NULL;
const char *type;
+ int i;
+/* Add here. The first matched one is used so put "better" instruction
+ * sets at the top.
+ */
#if HAVE_SSE
- /* Add here. The first matched one is used so put "better" instruction
- * sets at the top.
- */
-#elif HAVE_MMX
+ if(fptr == NULL && sse_available()) {
+ fptr = increment_sse;
+ type = "SSE";
+ }
+#endif
+#if HAVE_MMX
if(fptr == NULL && mmx_available()) {
fptr = increment_mmx;
type = "MMX";
@@ -29,7 +35,7 @@ int main(int argc, char **argv) {
}
printf("Using %s.\n", type);
fptr(four);
- for(int i=0; i<4; i++) {
+ for(i=0; i<4; i++) {
if(four[i] != expected[i]) {
printf("Increment function failed, got %f expected %f.\n", four[i], expected[i]);
return 1;