Implementation notes: amd64, h3neo, crypto_aead/norx6441v1

Compiler output

norx.c: In function 'norx_decrypt_lastblock',
norx.c:     inlined from 'norx_decrypt_msg' at norx.c:502:9,
norx.c:     inlined from 'norx_decrypt_msg' at norx.c:490:6:
norx.c: norx.c:313:16: warning: writing 1 byte into a region of size 0 [-Wstringop-overflow=]
norx.c:   313 |         b[j]   = c;
norx.c:       |         ~~~~~~~^~~
norx.c: norx.c: In function 'norx_decrypt_msg':
norx.c: norx.c:287:13: note: at offset 8 into destination object 'b' of size 8
norx.c:   287 |     uint8_t b[BYTES(NORX_W)];
norx.c:       |             ^
norx.c: In function 'norx_decrypt_lastblock',
norx.c:     inlined from 'norx_decrypt_msg' at norx.c:502:9,
norx.c:     inlined from 'norx_decrypt_msg' at norx.c:490:6,
norx.c:     inlined from 'norx_aead_decrypt' at norx.c:688:5:
norx.c: norx.c:313:16: warning: writing 1 byte into a region of size 0 [-Wstringop-overflow=]
norx.c:   313 |         b[j]   = c;
norx.c:       |         ~~~~~~~^~~
norx.c: norx.c: In function 'norx_aead_decrypt':
norx.c: norx.c:287:13: note: at offset 8 into destination object 'b' of size 8
norx.c:   287 |     uint8_t b[BYTES(NORX_W)];
norx.c:       |             ^

Compiler output

norx.c: norx.c:350:24: error: always_inline function '_mm256_loadu_si256' requires target feature 'avx', but would be inlined into function 'crypto_aead_norx6441v1_ymm_timingleaks_encrypt' that is compiled without support for 'avx'
norx.c:     const __m256i K  = LOADU(k + 0);
norx.c:                        ^
norx.c: norx.c:47:19: note: expanded from macro 'LOADU'
norx.c: #define LOADU(in) _mm256_loadu_si256((__m256i*)(in))
norx.c:                   ^
norx.c: norx.c:350:24: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
norx.c: norx.c:47:19: note: expanded from macro 'LOADU'
norx.c: #define LOADU(in) _mm256_loadu_si256((__m256i*)(in))
norx.c:                   ^
norx.c: norx.c:355:5: error: always_inline function '_mm256_castsi128_si256' requires target feature 'avx', but would be inlined into function 'crypto_aead_norx6441v1_ymm_timingleaks_encrypt' that is compiled without support for 'avx'
norx.c:     INITIALIZE(A, B, C, D, N, K);
norx.c:     ^
norx.c: norx.c:270:9: note: expanded from macro 'INITIALIZE'
norx.c:     A = _mm256_castsi128_si256(N);                                          \
norx.c:         ^
norx.c: norx.c:355:5: error: AVX vector return of type '__m256i' (vector of 4 'long long' values) without 'avx' enabled changes the ABI
norx.c: norx.c:270:9: note: expanded from macro 'INITIALIZE'
norx.c:     A = _mm256_castsi128_si256(N);                                          \
norx.c:         ^
norx.c: norx.c:355:5: error: '__builtin_ia32_insert128i256' needs target feature avx2
norx.c: norx.c:271:9: note: expanded from macro 'INITIALIZE'
norx.c:     A = _mm256_inserti128_si256(A, _mm_set_epi64x(U1, U0), 1);              \
norx.c:         ^
norx.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/avx2intrin.h:827:13: note: expanded from macro '_mm256_inserti128_si256'
norx.c: ...

Compiler output

norx.c: norx.c: In function 'crypto_aead_norx6441v1_ymm_timingleaks_encrypt':
norx.c: norx.c:350:19: warning: AVX vector return without AVX enabled changes the ABI [-Wpsabi]
norx.c:   350 |     const __m256i K  = LOADU(k + 0);
norx.c:       |                   ^
norx.c: In file included from /usr/lib/gcc/x86_64-linux-gnu/11/include/immintrin.h:43,
norx.c:                  from /usr/lib/gcc/x86_64-linux-gnu/11/include/x86intrin.h:32,
norx.c:                  from norx.c:26:
norx.c: norx.c: In function 'block_copy':
norx.c: /usr/lib/gcc/x86_64-linux-gnu/11/include/avxintrin.h:933:1: error: inlining failed in call to 'always_inline' '_mm256_storeu_si256': target specific option mismatch
norx.c:   933 | _mm256_storeu_si256 (__m256i_u *__P, __m256i __A)
norx.c:       | ^~~~~~~~~~~~~~~~~~~
norx.c: norx.c:48:24: note: called from here
norx.c:    48 | #define STOREU(out, x) _mm256_storeu_si256((__m256i*)(out), (x))
norx.c:       |                        ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
norx.c: norx.c:303:9: note: in expansion of macro 'STOREU'
norx.c:   303 |         STOREU(out + 32, LOADU(in + 32));
norx.c:       |         ^~~~~~
norx.c: In file included from /usr/lib/gcc/x86_64-linux-gnu/11/include/immintrin.h:43,
norx.c:                  from /usr/lib/gcc/x86_64-linux-gnu/11/include/x86intrin.h:32,
norx.c:                  from norx.c:26:
norx.c: /usr/lib/gcc/x86_64-linux-gnu/11/include/avxintrin.h:927:1: error: inlining failed in call to 'always_inline' '_mm256_loadu_si256': target specific option mismatch
norx.c:   927 | _mm256_loadu_si256 (__m256i_u const *__P)
norx.c:       | ^~~~~~~~~~~~~~~~~~
norx.c: norx.c:48:24: note: called from here
norx.c:    48 | #define STOREU(out, x) _mm256_storeu_si256((__m256i*)(out), (x))
norx.c: ...