Implementation notes: amd64, panther, crypto_sort/int32

Test failure

error 111

Compiler output

api.cpp: In file included from api.cpp:3:
api.cpp: In file included from ./aspas.h:204:
api.cpp: In file included from ./aspas.tcc:31:
api.cpp: In file included from ./sorter.h:120:
api.cpp: In file included from ./sorter_avx2.tcc:27:
api.cpp: ./util/extintrin.h:37:25: warning: unused variable 'max2' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                         ^
api.cpp: ./util/extintrin.h:37:13: warning: unused variable 'max1' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:             ^
api.cpp: ./util/extintrin.h:53:31: warning: unused variable 'min2' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                               ^
api.cpp: ./util/extintrin.h:53:19: warning: unused variable 'min1' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                   ^
api.cpp: In file included from api.cpp:3:
api.cpp: In file included from ./aspas.h:204:
api.cpp: In file included from ./aspas.tcc:32:
api.cpp: In file included from ./merger.h:64:
api.cpp: ./merger.tcc:187:17: warning: & has lower precedence than ==; == will be evaluated first [-Wparentheses]
api.cpp:         if (num & 1 == 1)
api.cpp:                 ^~~~~~~~
api.cpp: ./merger.tcc:187:17: note: place parentheses around the '==' expression to silence this warning
api.cpp: ...

Compiler output

api.cpp: In file included from api.cpp:3:
api.cpp: In file included from ./aspas.h:204:
api.cpp: In file included from ./aspas.tcc:31:
api.cpp: In file included from ./sorter.h:120:
api.cpp: In file included from ./sorter_avx2.tcc:27:
api.cpp: ./util/extintrin.h:37:13: warning: unused variable 'max1' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:             ^
api.cpp: ./util/extintrin.h:37:25: warning: unused variable 'max2' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                         ^
api.cpp: ./util/extintrin.h:53:31: warning: unused variable 'min2' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                               ^
api.cpp: ./util/extintrin.h:53:19: warning: unused variable 'min1' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                   ^
api.cpp: In file included from api.cpp:3:
api.cpp: In file included from ./aspas.h:204:
api.cpp: In file included from ./aspas.tcc:32:
api.cpp: In file included from ./merger.h:64:
api.cpp: ./merger.tcc:187:17: warning: & has lower precedence than ==; == will be evaluated first [-Wparentheses]
api.cpp:         if (num & 1 == 1)
api.cpp:                 ^~~~~~~~
api.cpp: ./merger.tcc:187:17: note: place parentheses around the '==' expression to silence this warning
api.cpp: ...

Compiler output

api.cpp: In file included from api.cpp:3:
api.cpp: In file included from ./aspas.h:204:
api.cpp: In file included from ./aspas.tcc:31:
api.cpp: In file included from ./sorter.h:120:
api.cpp: In file included from ./sorter_avx2.tcc:27:
api.cpp: ./util/extintrin.h:37:13: warning: unused variable 'max1' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:             ^
api.cpp: ./util/extintrin.h:37:25: warning: unused variable 'max2' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                         ^
api.cpp: ./util/extintrin.h:53:19: warning: unused variable 'min1' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                   ^
api.cpp: ./util/extintrin.h:53:31: warning: unused variable 'min2' [-Wunused-variable]
api.cpp:     __m128i max1, min1, max2, min2;
api.cpp:                               ^
api.cpp: In file included from api.cpp:3:
api.cpp: In file included from ./aspas.h:204:
api.cpp: In file included from ./aspas.tcc:32:
api.cpp: In file included from ./merger.h:64:
api.cpp: ./merger.tcc:187:17: warning: & has lower precedence than ==; == will be evaluated first [-Wparentheses]
api.cpp:         if (num & 1 == 1)
api.cpp:                 ^~~~~~~~
api.cpp: ./merger.tcc:187:17: note: place parentheses around the '==' expression to silence this warning
api.cpp: ...

Compiler output

api.cpp: In file included from sorter_avx2.tcc:27,
api.cpp:                  from sorter.h:120,
api.cpp:                  from aspas.tcc:31,
api.cpp:                  from aspas.h:204,
api.cpp:                  from api.cpp:3:
api.cpp: util/extintrin.h: In function '__m256i util::_my_mm256_min_epi32(__m256i, __m256i)':
api.cpp: util/extintrin.h:37:13: warning: unused variable 'max1' [-Wunused-variable]
api.cpp:    37 |     __m128i max1, min1, max2, min2;
api.cpp:       |             ^~~~
api.cpp: util/extintrin.h:37:25: warning: unused variable 'max2' [-Wunused-variable]
api.cpp:    37 |     __m128i max1, min1, max2, min2;
api.cpp:       |                         ^~~~
api.cpp: util/extintrin.h: In function '__m256i util::_my_mm256_max_epi32(__m256i, __m256i)':
api.cpp: util/extintrin.h:53:19: warning: unused variable 'min1' [-Wunused-variable]
api.cpp:    53 |     __m128i max1, min1, max2, min2;
api.cpp:       |                   ^~~~
api.cpp: util/extintrin.h:53:31: warning: unused variable 'min2' [-Wunused-variable]
api.cpp:    53 |     __m128i max1, min1, max2, min2;
api.cpp:       |                               ^~~~
api.cpp: In file included from sorter.h:120,
api.cpp:                  from aspas.tcc:31,
api.cpp:                  from aspas.h:204,
api.cpp:                  from api.cpp:3:
api.cpp: sorter_avx2.tcc: At global scope:
api.cpp: sorter_avx2.tcc:96:47: warning: ignoring attributes on template argument '__m256' [-Wignored-attributes]
api.cpp: ...

Compiler output

sort.c: sort.c:940:40: error: always_inline function '_mm256_set1_epi32' requires target feature 'avx', but would be inlined into function 'int32_sort' that is compiled without support for 'avx'
sort.c:     for (i = q>>3;i < q>>2;++i) y[i] = _mm256_set1_epi32(0x7fffffff);
sort.c:                                        ^
sort.c: sort.c:940:40: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
sort.c: sort.c:956:22: error: always_inline function '_mm256_loadu_si256' requires target feature 'avx', but would be inlined into function 'int32_sort' that is compiled without support for 'avx'
sort.c:         int32x8 x0 = int32x8_load(&x[i]);
sort.c:                      ^
sort.c: sort.c:9:25: note: expanded from macro 'int32x8_load'
sort.c: #define int32x8_load(z) _mm256_loadu_si256((__m256i *) (z))
sort.c:                         ^
sort.c: sort.c:956:22: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
sort.c: sort.c:9:25: note: expanded from macro 'int32x8_load'
sort.c: #define int32x8_load(z) _mm256_loadu_si256((__m256i *) (z))
sort.c:                         ^
sort.c: sort.c:957:22: error: always_inline function '_mm256_loadu_si256' requires target feature 'avx', but would be inlined into function 'int32_sort' that is compiled without support for 'avx'
sort.c:         int32x8 x1 = int32x8_load(&x[i+q]);
sort.c:                      ^
sort.c: sort.c:9:25: note: expanded from macro 'int32x8_load'
sort.c: #define int32x8_load(z) _mm256_loadu_si256((__m256i *) (z))
sort.c:                         ^
sort.c: sort.c:957:22: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
sort.c: sort.c:9:25: note: expanded from macro 'int32x8_load'
sort.c: #define int32x8_load(z) _mm256_loadu_si256((__m256i *) (z))
sort.c:                         ^
sort.c: sort.c:958:22: error: always_inline function '_mm256_loadu_si256' requires target feature 'avx', but would be inlined into function 'int32_sort' that is compiled without support for 'avx'
sort.c: ...

Compiler output

sort.c: sort.c:133:17: warning: passing 'int32 [n]' to parameter of type 'uint32 *' (aka 'unsigned int *') converts between pointers to integer types with different sign [-Wpointer-sign]
sort.c:   RadixSort11(x,y,n);
sort.c:                 ^
sort.c: sort.c:47:48: note: passing argument to parameter 'sort' here
sort.c: static void RadixSort11(uint32 *array, uint32 *sort, uint32 elements)
sort.c:                                                ^
sort.c: 1 warning generated.

Compiler output

sort.c: sort.c: In function 'crypto_sort_int32_herf_timingleaks':
sort.c: sort.c:133:17: warning: pointer targets in passing argument 2 of 'RadixSort11' differ in signedness [-Wpointer-sign]
sort.c:   133 |   RadixSort11(x,y,n);
sort.c:       |                 ^
sort.c:       |                 |
sort.c:       |                 int32 * {aka int *}
sort.c: sort.c:47:48: note: expected 'uint32 *' {aka 'unsigned int *'} but argument is of type 'int32 *' {aka 'int *'}
sort.c:    47 | static void RadixSort11(uint32 *array, uint32 *sort, uint32 elements)
sort.c:       |                                        ~~~~~~~~^~~~

Compiler output

int32_sort.c: int32_sort.c:330:15: error: always_inline function '_mm256_loadu_si256' requires target feature 'avx', but would be inlined into function 'minmax8' that is compiled without support for 'avx'
int32_sort.c:   __m256i a = _mm256_loadu_si256((__m256i *) x);
int32_sort.c:               ^
int32_sort.c: int32_sort.c:330:15: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
int32_sort.c: int32_sort.c:331:15: error: always_inline function '_mm256_loadu_si256' requires target feature 'avx', but would be inlined into function 'minmax8' that is compiled without support for 'avx'
int32_sort.c:   __m256i b = _mm256_loadu_si256((__m256i *) y);
int32_sort.c:               ^
int32_sort.c: int32_sort.c:331:15: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
int32_sort.c: int32_sort.c:332:37: error: always_inline function '_mm256_min_epi32' requires target feature 'avx2', but would be inlined into function 'minmax8' that is compiled without support for 'avx2'
int32_sort.c:   _mm256_storeu_si256((__m256i *) x,_mm256_min_epi32(a,b));
int32_sort.c:                                     ^
int32_sort.c: int32_sort.c:332:37: error: AVX vector argument of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
int32_sort.c: int32_sort.c:332:3: error: always_inline function '_mm256_storeu_si256' requires target feature 'avx', but would be inlined into function 'minmax8' that is compiled without support for 'avx'
int32_sort.c:   _mm256_storeu_si256((__m256i *) x,_mm256_min_epi32(a,b));
int32_sort.c:   ^
int32_sort.c: int32_sort.c:332:3: error: AVX vector argument of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
int32_sort.c: int32_sort.c:333:37: error: always_inline function '_mm256_max_epi32' requires target feature 'avx2', but would be inlined into function 'minmax8' that is compiled without support for 'avx2'
int32_sort.c:   _mm256_storeu_si256((__m256i *) y,_mm256_max_epi32(a,b));
int32_sort.c:                                     ^
int32_sort.c: int32_sort.c:333:37: error: AVX vector argument of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
int32_sort.c: int32_sort.c:333:3: error: always_inline function '_mm256_storeu_si256' requires target feature 'avx', but would be inlined into function 'minmax8' that is compiled without support for 'avx'
int32_sort.c:   _mm256_storeu_si256((__m256i *) y,_mm256_max_epi32(a,b));
int32_sort.c:   ^
int32_sort.c: int32_sort.c:333:3: error: AVX vector argument of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
int32_sort.c: int32_sort.c:364:34: error: always_inline function '_mm_min_epi32' requires target feature 'sse4.1', but would be inlined into function 'minmax4' that is compiled without support for 'sse4.1'
int32_sort.c: ...

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x401F70
   at 0x...: st32 (try-anything.c:47)
   by 0x...: core (try-anything.c:78)
   by 0x...: salsa20 (try-anything.c:101)
   by 0x...: testvector (try-anything.c:124)
   by 0x...: myrandom (try-anything.c:132)
   by 0x...: test (try.c:104)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x403EB8
   at 0x...: int32_sort_2power (sort.c:486)
   by 0x...: int32_sort (sort.c:947)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x4035AA
   at 0x...: int32_sort_2power (sort.c:486)
   by 0x...: int32_sort (sort.c:947)
   by 0x...: crypto_sort_int32_avx2_constbranchindex (sort.c:1189)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x4019A6
   at 0x...: core (try-anything.c:73)
   by 0x...: salsa20 (try-anything.c:101)
   by 0x...: testvector (try-anything.c:124)
   by 0x...: myrandom (try-anything.c:132)
   by 0x...: test (try.c:104)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x109B69
   at 0x...: salsa20.part.0 (try-anything.c:102)
   by 0x...: salsa20 (try-anything.c:85)
   by 0x...: canary (try-anything.c:148)
   by 0x...: input_prepare (try-anything.c:163)
   by 0x...: test (try.c:107)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x109A0A
   at 0x...: st32 (try-anything.c:47)
   by 0x...: core (try-anything.c:78)
   by 0x...: salsa20 (try-anything.c:101)
   by 0x...: salsa20 (try-anything.c:81)
   by 0x...: testvector (try-anything.c:124)
   by 0x...: myrandom (try-anything.c:132)
   by 0x...: test (try.c:104)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x10A528
   at 0x...: int32_sort_2power (sort.c:372)
   by 0x...: int32_sort (sort.c:947)
   by 0x...: crypto_sort_int32_avx2_constbranchindex (sort.c:1189)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x10A553
   at 0x...: int32_sort_2power (sort.c:372)
   by 0x...: int32_sort (sort.c:947)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x402F56
   at 0x...: minmax02134657 (int32_sort.c:36)
   by 0x...: multiminmax2plus2 (int32_sort.c:50)
   by 0x...: crypto_sort_int32_oldavx2_constbranchindex (int32_sort.c:406)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x402B32
   at 0x...: minmax02134657 (int32_sort.c:36)
   by 0x...: multiminmax2plus2 (int32_sort.c:50)
   by 0x...: crypto_sort_int32_oldavx2_constbranchindex (int32_sort.c:406)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x10A4AA
   at 0x...: _mm256_cmpgt_epi32 (avx2intrin.h:275)
   by 0x...: minmax02134657 (int32_sort.c:33)
   by 0x...: multiminmax2plus2 (int32_sort.c:50)
   by 0x...: crypto_sort_int32_oldavx2_constbranchindex (int32_sort.c:406)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x109EFA
   at 0x...: _mm256_cmpgt_epi32 (avx2intrin.h:275)
   by 0x...: minmax02134657 (int32_sort.c:33)
   by 0x...: multiminmax2plus2 (int32_sort.c:50)
   by 0x...: crypto_sort_int32_oldavx2_constbranchindex (int32_sort.c:406)
   by 0x...: test (try.c:112)
   by 0x...: main (try-anything.c:345)

Passed TIMECOP

TIMECOP iterations: 10