Implementation notes: amd64, margaux, crypto_stream/speck128128ctr

Computer: margaux
Microarchitecture: amd64; C2 65nm (6fb)
Architecture: amd64
CPU ID: GenuineIntel-000006fb-bfebfbff
SUPERCOP version: 20221122
Operation: crypto_stream
Primitive: speck128128ctr

Time	Object size	Test size	Implementation	Compiler	Benchmark date	SUPERCOP version
7317	34318 0 0	50369 804 1000	`T:sse4`	`gcc_-march=native_-mtune=native_-O3_-fomit-frame-pointer_-fwrapv_-fPIC_-fPIE`	20210503	20210423
7590	29787 0 0	41866 796 968	`T:sse4`	`clang_-march=native_-Os_-fomit-frame-pointer_-fwrapv_-Qunused-arguments_-fPIC_-fPIE`	20210503	20210423
7592	31316 0 0	46684 804 968	`T:sse4`	`clang_-march=native_-O3_-fomit-frame-pointer_-fwrapv_-Qunused-arguments_-fPIC_-fPIE`	20210503	20210423
7593	31316 0 0	45340 804 968	`T:sse4`	`clang_-march=native_-O2_-fomit-frame-pointer_-fwrapv_-Qunused-arguments_-fPIC_-fPIE`	20210503	20210423
7598	31316 0 0	45340 804 968	`T:sse4`	`clang_-march=native_-O_-fomit-frame-pointer_-fwrapv_-Qunused-arguments_-fPIC_-fPIE`	20210503	20210423
8104	35079 0 0	48520 796 1000	`T:sse4`	`gcc_-march=native_-mtune=native_-O_-fomit-frame-pointer_-fwrapv_-fPIC_-fPIE`	20210503	20210423
13162	18001 0 0	31624 796 1000	`T:sse4`	`gcc_-march=native_-mtune=native_-O2_-fomit-frame-pointer_-fwrapv_-fPIC_-fPIE`	20210503	20210423
13239	15656 0 0	28084 780 968	`T:sse4`	`gcc_-march=native_-mtune=native_-Os_-fomit-frame-pointer_-fwrapv_-fPIC_-fPIE`	20210503	20210423

Compiler output

Implementation: T:avx2
Security model: timingleaks
Compiler: clang -march=native -O2 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE

stream.c: stream.c:288:3: error: always_inline function '_mm256_set_epi64x' requires target feature 'xsave', but would be inlined into function 'ExpandKey' that is compiled without support for 'xsave'
stream.c: EK(A,B,rk,key);
stream.c: ^
stream.c: ./Speck128128AVX2.h:54:24: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX2.h:52:28: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX2_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c))
stream.c: ^
stream.c: ./Intrinsics_AVX2_128block.h:24:13: note: expanded from macro 'SET'
stream.c: #define SET _mm256_set_epi64x
stream.c: ^
stream.c: stream.c:288:3: error: always_inline function '_mm256_set_epi64x' requires target feature 'xsave', but would be inlined into function 'ExpandKey' that is compiled without support for 'xsave'
stream.c: ./Speck128128AVX2.h:54:42: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX2.h:52:28: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX2_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c))
stream.c: ^
stream.c: ...

Number of similar (compiler,implementation) pairs: 4, namely:

Compiler	Implementations
clang -march=native -O2 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx2
clang -march=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx2
clang -march=native -O -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx2
clang -march=native -Os -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx2

Compiler output

Implementation: T:avx2
Security model: timingleaks
Compiler: clang -mcpu=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE

stream.c: stream.c:288:3: error: always_inline function '_mm256_set_epi64x' requires target feature 'sse4.2', but would be inlined into function 'ExpandKey' that is compiled without support for 'sse4.2'
stream.c: EK(A,B,rk,key);
stream.c: ^
stream.c: ./Speck128128AVX2.h:54:24: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX2.h:52:28: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX2_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c))
stream.c: ^
stream.c: ./Intrinsics_AVX2_128block.h:24:13: note: expanded from macro 'SET'
stream.c: #define SET _mm256_set_epi64x
stream.c: ^
stream.c: stream.c:288:3: error: always_inline function '_mm256_set_epi64x' requires target feature 'sse4.2', but would be inlined into function 'ExpandKey' that is compiled without support for 'sse4.2'
stream.c: ./Speck128128AVX2.h:54:42: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX2.h:52:28: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX2_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c))
stream.c: ^
stream.c: ...

Number of similar (compiler,implementation) pairs: 1, namely:

Compiler	Implementations
clang -mcpu=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx2

Compiler output

Implementation: T:avx2
Security model: timingleaks
Compiler: gcc -march=native -mtune=native -O2 -fomit-frame-pointer -fwrapv -fPIC -fPIE

stream.c: In file included from Speck128128AVX2.h:17:0,
stream.c: from stream.c:20:
stream.c: stream.c: In function 'Encrypt':
stream.c: Intrinsics_AVX2_128block.h:25:21: warning: AVX vector return without AVX enabled changes the ABI [-Wpsabi]
stream.c: #define SET1(X,c) (X=SET(c,c,c,c))
stream.c: ~~^~~~~~~~~~~~~~
stream.c: stream.c:128:3: note: in expansion of macro 'SET1'
stream.c: SET1(X[0],nonce[1]); SET4(Y[0],nonce[0]);
stream.c: ^~~~
stream.c: In file included from /usr/lib/gcc/x86_64-linux-gnu/7/include/immintrin.h:43:0,
stream.c: from Intrinsics_AVX2_128block.h:5,
stream.c: from Speck128128AVX2.h:17,
stream.c: from stream.c:20:
stream.c: /usr/lib/gcc/x86_64-linux-gnu/7/include/avx2intrin.h:126:1: error: inlining failed in call to always_inline '_mm256_add_epi64': target specific option mismatch
stream.c: _mm256_add_epi64 (__m256i __A, __m256i __B)
stream.c: ^~~~~~~~~~~~~~~~
stream.c: In file included from Speck128128AVX2.h:17:0,
stream.c: from stream.c:20:
stream.c: Intrinsics_AVX2_128block.h:17:13: note: called from here
stream.c: #define ADD _mm256_add_epi64
stream.c: ^
stream.c: Intrinsics_AVX2_128block.h:26:38: note: in expansion of macro 'ADD'
stream.c: #define SET4(X,c) (X=SET(c,c,c,c), X=ADD(X,_q))
stream.c: ^~~
stream.c: stream.c:128:24: note: in expansion of macro 'SET4'
stream.c: ...

Number of similar (compiler,implementation) pairs: 4, namely:

Compiler	Implementations
gcc -march=native -mtune=native -O2 -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx2
gcc -march=native -mtune=native -O3 -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx2
gcc -march=native -mtune=native -O -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx2
gcc -march=native -mtune=native -Os -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx2

Compiler output

Implementation: T:avx512
Security model: timingleaks
Compiler: clang -march=native -O2 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE

stream.c: stream.c:329:3: error: always_inline function '_mm512_set_epi64' requires target feature 'avx512f', but would be inlined into function 'ExpandKey' that is compiled without support for 'avx512f'
stream.c: EK(A,B,rk,key);
stream.c: ^
stream.c: ./Speck128128AVX512.h:59:24: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX512.h:57:26: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX512_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c,c,c,c,c))
stream.c: ^
stream.c: ./Intrinsics_AVX512_128block.h:16:13: note: expanded from macro 'SET'
stream.c: #define SET _mm512_set_epi64
stream.c: ^
stream.c: stream.c:329:3: error: always_inline function '_mm512_set_epi64' requires target feature 'avx512f', but would be inlined into function 'ExpandKey' that is compiled without support for 'avx512f'
stream.c: ./Speck128128AVX512.h:59:42: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX512.h:57:26: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX512_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c,c,c,c,c))
stream.c: ^
stream.c: ...

Number of similar (compiler,implementation) pairs: 4, namely:

Compiler	Implementations
clang -march=native -O2 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx512
clang -march=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx512
clang -march=native -O -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx512
clang -march=native -Os -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx512

Compiler output

Implementation: T:avx512
Security model: timingleaks
Compiler: clang -mcpu=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE

stream.c: stream.c:329:3: error: always_inline function '_mm512_set_epi64' requires target feature 'avx2', but would be inlined into function 'ExpandKey' that is compiled without support for 'avx2'
stream.c: EK(A,B,rk,key);
stream.c: ^
stream.c: ./Speck128128AVX512.h:59:24: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX512.h:57:26: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX512_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c,c,c,c,c))
stream.c: ^
stream.c: ./Intrinsics_AVX512_128block.h:16:13: note: expanded from macro 'SET'
stream.c: #define SET _mm512_set_epi64
stream.c: ^
stream.c: stream.c:329:3: error: always_inline function '_mm512_set_epi64' requires target feature 'avx2', but would be inlined into function 'ExpandKey' that is compiled without support for 'avx2'
stream.c: ./Speck128128AVX512.h:59:42: note: expanded from macro 'EK'
stream.c: #define EK(A,B,k,key) (RK(B,A,k,key,0), RK(B,A,k,key,1), RK(B,A,k,key,2), RK(B,A,k,key,3), RK(B,A,k,key,4), RK(B,A,k,key,5), RK(B,A,k,key,6), \
stream.c: ^
stream.c: ./Speck128128AVX512.h:57:26: note: expanded from macro 'RK'
stream.c: #define RK(X,Y,k,key,i) (SET1(k[i],Y), key[i]=Y, X=RCS(X,8), X+=Y, X^=i, Y=LCS(Y,3), Y^=X)
stream.c: ^
stream.c: ./Intrinsics_AVX512_128block.h:25:22: note: expanded from macro 'SET1'
stream.c: #define SET1(X,c) (X=SET(c,c,c,c,c,c,c,c))
stream.c: ^
stream.c: ...

Number of similar (compiler,implementation) pairs: 1, namely:

Compiler	Implementations
clang -mcpu=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:avx512

Compiler output

Implementation: T:avx512
Security model: timingleaks
Compiler: gcc -march=native -mtune=native -O2 -fomit-frame-pointer -fwrapv -fPIC -fPIE

stream.c: In file included from Speck128128AVX512.h:17:0,
stream.c: from stream.c:21:
stream.c: stream.c: In function 'Encrypt':
stream.c: Intrinsics_AVX512_128block.h:25:21: warning: AVX512F vector return without AVX512F enabled changes the ABI [-Wpsabi]
stream.c: #define SET1(X,c) (X=SET(c,c,c,c,c,c,c,c))
stream.c: ~~^~~~~~~~~~~~~~~~~~~~~~
stream.c: stream.c:135:5: note: in expansion of macro 'SET1'
stream.c: SET1(X[0],nonce[1]); SET8(Y[0],nonce[0]);
stream.c: ^~~~
stream.c: In file included from /usr/lib/gcc/x86_64-linux-gnu/7/include/immintrin.h:45:0,
stream.c: from Intrinsics_AVX512_128block.h:5,
stream.c: from Speck128128AVX512.h:17,
stream.c: from stream.c:21:
stream.c: /usr/lib/gcc/x86_64-linux-gnu/7/include/avx512fintrin.h:5831:1: error: inlining failed in call to always_inline '_mm512_storeu_si512': target specific option mismatch
stream.c: _mm512_storeu_si512 (void *__P, __m512i __A)
stream.c: ^~~~~~~~~~~~~~~~~~~
stream.c: In file included from Speck128128AVX512.h:17:0,
stream.c: from stream.c:21:
stream.c: Intrinsics_AVX512_128block.h:32:18: note: called from here
stream.c: #define ST(ip,X) _mm512_storeu_si512((void *)(ip),X)
stream.c: ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
stream.c: Intrinsics_AVX512_128block.h:33:43: note: in expansion of macro 'ST'
stream.c: #define STORE(out,X,Y) (ST(out,LOW(Y,X)), ST(out+64,HIGH(Y,X)))
stream.c: ^~
stream.c: stream.c:138:5: note: in expansion of macro 'STORE'
stream.c: ...

Number of similar (compiler,implementation) pairs: 4, namely:

Compiler	Implementations
gcc -march=native -mtune=native -O2 -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx512
gcc -march=native -mtune=native -O3 -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx512
gcc -march=native -mtune=native -O -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx512
gcc -march=native -mtune=native -Os -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:avx512

Compiler output

Implementation: T:sse4
Security model: timingleaks
Compiler: clang -mcpu=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE

stream.c: stream.c:114:21: error: always_inline function '_mm_shuffle_epi8' requires target feature 'ssse3', but would be inlined into function 'Encrypt' that is compiled without support for 'ssse3'
stream.c: if (numbytes==32) Enc(X,Y,rk,2);
stream.c: ^
stream.c: ./Speck128128SSE4.h:42:23: note: expanded from macro 'Enc'
stream.c: #define Enc(X,Y,k,n) (Rx##n(X,Y,k[0]), Rx##n(X,Y,k[1]), Rx##n(X,Y,k[2]), Rx##n(X,Y,k[3]), Rx##n(X,Y,k[4]), Rx##n(X,Y,k[5]), Rx##n(X,Y,k[6]), Rx##n(X,Y,k[7]), \
stream.c: ^
stream.c: <scratch space>:91:1: note: expanded from here
stream.c: Rx2
stream.c: ^
stream.c: ./Speck128128SSE4.h:25:21: note: expanded from macro 'Rx2'
stream.c: #define Rx2(X,Y,k) (R(X[0],Y[0],k))
stream.c: ^
stream.c: ./Speck128128SSE4.h:23:29: note: expanded from macro 'R'
stream.c: #define R(X,Y,k) (X=XOR(ADD(ROR8(X),Y),k), Y=XOR(ROL(Y,3),X))
stream.c: ^
stream.c: ./Intrinsics_SSE4_128block.h:41:19: note: expanded from macro 'ROR8'
stream.c: #define ROR8(X) (SHFL(X,R8))
stream.c: ^
stream.c: ./Intrinsics_SSE4_128block.h:37:14: note: expanded from macro 'SHFL'
stream.c: #define SHFL _mm_shuffle_epi8
stream.c: ^
stream.c: stream.c:114:21: error: always_inline function '_mm_shuffle_epi8' requires target feature 'ssse3', but would be inlined into function 'Encrypt' that is compiled without support for 'ssse3'
stream.c: ./Speck128128SSE4.h:42:41: note: expanded from macro 'Enc'
stream.c: #define Enc(X,Y,k,n) (Rx##n(X,Y,k[0]), Rx##n(X,Y,k[1]), Rx##n(X,Y,k[2]), Rx##n(X,Y,k[3]), Rx##n(X,Y,k[4]), Rx##n(X,Y,k[5]), Rx##n(X,Y,k[6]), Rx##n(X,Y,k[7]), \
stream.c: ^
stream.c: ...

Number of similar (compiler,implementation) pairs: 1, namely:

Compiler	Implementations
clang -mcpu=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:sse4

Namespace violations

Implementation: T:sse4
Security model: timingleaks
Compiler: clang -march=native -O2 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE

stream.o Encrypt T
stream.o Encrypt_Xor T
stream.o ExpandKey T

Number of similar (compiler,implementation) pairs: 8, namely:

Compiler	Implementations
clang -march=native -O2 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:sse4
clang -march=native -O3 -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:sse4
clang -march=native -O -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:sse4
clang -march=native -Os -fomit-frame-pointer -fwrapv -Qunused-arguments -fPIC -fPIE	T:sse4
gcc -march=native -mtune=native -O2 -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:sse4
gcc -march=native -mtune=native -O3 -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:sse4
gcc -march=native -mtune=native -O -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:sse4
gcc -march=native -mtune=native -Os -fomit-frame-pointer -fwrapv -fPIC -fPIE	T:sse4