Implementation notes: amd64, h3neo, crypto_kem/mceliece348864pcf

Compiler output

decrypt.c: decrypt.c:220:11: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
decrypt.c:         allone = vec256_set1_16b(0xFFFF);
decrypt.c:                  ^
decrypt.c: decrypt.c:224:17: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
decrypt.c:                 error256[i] = vec256_or_reduce(eval[i]);
decrypt.c:                               ^
decrypt.c: decrypt.c:225:17: warning: AVX vector argument of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
decrypt.c:                 error256[i] = vec256_xor(error256[i], allone);
decrypt.c:                               ^
decrypt.c: decrypt.c:153:12: warning: AVX vector return of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
decrypt.c:                 out[i] = vec256_set4x(v[0], v[1], v[2], v[3]);
decrypt.c:                          ^
decrypt.c: In file included from decrypt.c:15:
decrypt.c: In file included from ./fft_tr.h:11:
decrypt.c: ./vec256.h:35:10: error: always_inline function '_mm256_set_epi64x' requires target feature 'avx', but would be inlined into function 'vec256_set4x' that is compiled without support for 'avx'
decrypt.c:         return  _mm256_set_epi64x(a3, a2, a1, a0);
decrypt.c:                 ^
decrypt.c: ./vec256.h:35:10: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
decrypt.c: decrypt.c:59:15: warning: AVX vector argument of type 'vec256' (aka '__m256i') without 'avx' enabled changes the ABI [-Wpsabi]
decrypt.c:                 out[i][j] = vec256_and(inv[i][j], recv[i]);
decrypt.c:                             ^
decrypt.c: In file included from decrypt.c:15:
decrypt.c: In file included from ./fft_tr.h:11:
decrypt.c: ./vec256.h:74:9: error: always_inline function '_mm256_and_si256' requires target feature 'avx2', but would be inlined into function 'vec256_and' that is compiled without support for 'avx2'
decrypt.c:         return _mm256_and_si256(a, b);
decrypt.c: ...

Compiler output

benes.c: In file included from transpose.h:11,
benes.c:                  from benes.c:14:
benes.c: vec256.h: In function 'vec256_load':
benes.c: vec256.h:14:1: warning: AVX vector return without AVX enabled changes the ABI [-Wpsabi]
benes.c:    14 | {
benes.c:       | ^
bm.c: In file included from vec128.h:9,
bm.c:                  from bm.h:12,
bm.c:                  from bm.c:24:
bm.c: bm.c: In function 'get_coefs':
bm.c: /usr/lib/gcc/x86_64-linux-gnu/11/include/smmintrin.h:455:1: error: inlining failed in call to 'always_inline' '_mm_extract_epi64': target specific option mismatch
bm.c:   455 | _mm_extract_epi64 (__m128i __X, const int __N)
bm.c:       | ^~~~~~~~~~~~~~~~~
bm.c: In file included from bm.h:12,
bm.c:                  from bm.c:24:
bm.c: vec128.h:23:42: note: called from here
bm.c:    23 | #define vec128_extract(a, i) ((uint64_t) _mm_extract_epi64((vec128) (a), (i)))
bm.c:       |                                          ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
bm.c: bm.c:122:44: note: in expansion of macro 'vec128_extract'
bm.c:   122 |                 out[ (4*1 + k)*16 + i ] = (vec128_extract(buf[i], 1) >> (k*16)) & GFMASK;
bm.c:       |                                            ^~~~~~~~~~~~~~
bm.c: In file included from vec128.h:9,
bm.c:                  from bm.h:12,
bm.c:                  from bm.c:24:
bm.c: /usr/lib/gcc/x86_64-linux-gnu/11/include/smmintrin.h:455:1: error: inlining failed in call to 'always_inline' '_mm_extract_epi64': target specific option mismatch
bm.c:   455 | _mm_extract_epi64 (__m128i __X, const int __N)
bm.c:       | ^~~~~~~~~~~~~~~~~
bm.c: In file included from bm.h:12,
bm.c:                  from bm.c:24:
bm.c: vec128.h:23:42: note: called from here
bm.c:    23 | #define vec128_extract(a, i) ((uint64_t) _mm_extract_epi64((vec128) (a), (i)))
bm.c: ...

Compiler output

decrypt.c: In file included from decrypt.c:9:
decrypt.c: In file included from ./vec128_gf.h:10:
decrypt.c: ./vec128.h:33:9: error: always_inline function '_mm_testz_si128' requires target feature 'sse4.1', but would be inlined into function 'vec128_testz' that is compiled without support for 'sse4.1'
decrypt.c:         return _mm_testz_si128(a, a);
decrypt.c:                ^
decrypt.c: 1 error generated.

Compiler output

bm.c: bm.c:120:18: warning: argument 1 of type 'uint64_t[12]' {aka 'long unsigned int[12]'} with mismatched bound [-Warray-parameter=]
bm.c:   120 | void bm(uint64_t out[ GFBITS ], vec128 in[ GFBITS ])
bm.c:       |         ~~~~~~~~~^~~~~~~~~~~~~
bm.c: In file included from bm.c:15:
bm.c: bm.h:15:19: note: previously declared as 'uint64_t *' {aka 'long unsigned int *'}
bm.c:    15 | void bm(uint64_t *out, vec128 *in);
bm.c:       |         ~~~~~~~~~~^~~
bm.c: bm.c:120:40: warning: argument 2 of type 'vec128[12]' {aka '__m128i[12]'} with mismatched bound [-Warray-parameter=]
bm.c:   120 | void bm(uint64_t out[ GFBITS ], vec128 in[ GFBITS ])
bm.c:       |                                 ~~~~~~~^~~~~~~~~~~~
bm.c: In file included from bm.c:15:
bm.c: bm.h:15:32: note: previously declared as 'vec128 *' {aka '__m128i *'}
bm.c:    15 | void bm(uint64_t *out, vec128 *in);
bm.c:       |                        ~~~~~~~~^~
bm.c: In file included from vec128.h:10,
bm.c:                  from bm.h:13,
bm.c:                  from bm.c:15:
bm.c: bm.c: In function 'get_coefs':
bm.c: /usr/lib/gcc/x86_64-linux-gnu/11/include/smmintrin.h:455:1: error: inlining failed in call to 'always_inline' '_mm_extract_epi64': target specific option mismatch
bm.c:   455 | _mm_extract_epi64 (__m128i __X, const int __N)
bm.c:       | ^~~~~~~~~~~~~~~~~
bm.c: In file included from bm.h:13,
bm.c:                  from bm.c:15:
bm.c: vec128.h:29:42: note: called from here
bm.c:    29 | #define vec128_extract(a, i) ((uint64_t) _mm_extract_epi64((vec128) (a), (i)))
bm.c: ...

TIMECOP error (can be valgrind bug)

error 111

Process terminating with default action of signal 4 (SIGILL)
 Illegal opcode at address 0x10E5CB
   at 0x...: syndrome (encrypt.c:116)
   by 0x...: crypto_kem_mceliece348864pcf_ref_constbranchindex_pke_encrypt (encrypt.c:134)
   by 0x...: crypto_kem_mceliece348864pcf_ref_constbranchindex_operation_enc (kem_enc.c:30)
   by 0x...: test (try.c:141)
   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 0x1101FB
   at 0x...: syndrome (encrypt.c:116)
   by 0x...: crypto_kem_mceliece348864pcf_ref_constbranchindex_pke_encrypt (encrypt.c:134)
   by 0x...: crypto_kem_mceliece348864pcf_ref_constbranchindex_operation_enc (kem_enc.c:30)
   by 0x...: test (try.c:141)
   by 0x...: main (try-anything.c:345)

Passed TIMECOP

TIMECOP iterations: 1