Add a linker test re: section alignment
authorArtem Pyanykh <artempyanykh@gmail.com>
Mon, 11 Feb 2019 11:05:34 +0000 (14:05 +0300)
committerMarge Bot <ben+marge-bot@smart-cactus.org>
Wed, 20 Mar 2019 23:52:39 +0000 (19:52 -0400)
testsuite/tests/rts/linker/Makefile
testsuite/tests/rts/linker/aligned_mem_access.c [new file with mode: 0644]
testsuite/tests/rts/linker/aligned_mem_access.stdout [new file with mode: 0644]
testsuite/tests/rts/linker/all.T

index 838a83a..2320d34 100644 (file)
@@ -6,3 +6,8 @@ unsigned_reloc_macho_x64:
        as -o unsigned_reloc_macho_x64.o unsigned_reloc_macho_x64.s
        '$(TEST_HC)' $(TEST_HC_OPTS_NO_RTSOPTS) -v0 --make -no-rtsopts-suggestions -no-hs-main -o runner runner.c
        ./runner unsigned_reloc_macho_x64.o getAnswer
+
+aligned_mem_access:
+       cc -c -o aligned_mem_access.o aligned_mem_access.c
+       '$(TEST_HC)' $(TEST_HC_OPTS_NO_RTSOPTS) -v0 --make -no-rtsopts-suggestions -no-hs-main -o runner runner.c
+       ./runner aligned_mem_access.o foo
diff --git a/testsuite/tests/rts/linker/aligned_mem_access.c b/testsuite/tests/rts/linker/aligned_mem_access.c
new file mode 100644 (file)
index 0000000..cef90c3
--- /dev/null
@@ -0,0 +1,14 @@
+#include <stdio.h>
+#include <immintrin.h>
+
+__m128 mvec   = {1.0, 2.0, 3.0, 42.0};
+float  fvec[] = {.0, .0, .0, .0};
+
+/* Uses movaps instruction to move data between XMMn <-> mem. Fails
+ * with segfault when data section is not properly aligned (16 byte).
+ */
+long foo(void)
+{
+        _mm_store_ps(fvec, mvec);
+        return (long) fvec[3];
+}
diff --git a/testsuite/tests/rts/linker/aligned_mem_access.stdout b/testsuite/tests/rts/linker/aligned_mem_access.stdout
new file mode 100644 (file)
index 0000000..4b728c2
--- /dev/null
@@ -0,0 +1,2 @@
+Linking: path = aligned_mem_access.o, symname = _foo
+42
\ No newline at end of file
index 66c2156..23d79d3 100644 (file)
@@ -7,3 +7,10 @@ test('unsigned_reloc_macho_x64',
          unless(arch('x86_64'), skip)
      ],
      run_command, ['$MAKE -s --no-print-directory unsigned_reloc_macho_x64'])
+
+test('aligned_mem_access',
+     [
+         extra_files(['runner.c', 'aligned_mem_access.c']),
+         unless(opsys('darwin') and arch('x86_64'), expect_broken(13624))
+     ],
+     run_command, ['$MAKE -s --no-print-directory aligned_mem_access'])