Implementation notes: aarch64, pi4b, crypto_stream/chacha12

Compiler output

chacha.S: chacha.S:19:5: error: unknown token in expression
chacha.S: mov %rsp,%r11
chacha.S:     ^
chacha.S: chacha.S:19:5: error: invalid operand
chacha.S: mov %rsp,%r11
chacha.S:     ^
chacha.S: chacha.S:20:9: error: unknown token in expression
chacha.S: and $31,%r11
chacha.S:         ^
chacha.S: chacha.S:20:9: error: invalid operand
chacha.S: and $31,%r11
chacha.S:         ^
chacha.S: chacha.S:21:10: error: unknown token in expression
chacha.S: add $384,%r11
chacha.S:          ^
chacha.S: chacha.S:21:10: error: invalid operand
chacha.S: add $384,%r11
chacha.S:          ^
chacha.S: chacha.S:22:5: error: unknown token in expression
chacha.S: sub %r11,%rsp
chacha.S:     ^
chacha.S: chacha.S:22:5: error: invalid operand
chacha.S: sub %r11,%rsp
chacha.S:     ^
chacha.S: chacha.S:23:5: error: unknown token in expression
chacha.S: ...

Compiler output

chacha.S: chacha.S: Assembler messages:
chacha.S: chacha.S:19: Error: operand 1 must be an integer register -- `mov %rsp,%r11'
chacha.S: chacha.S:20: Error: operand 1 must be an integer or stack pointer register -- `and $31,%r11'
chacha.S: chacha.S:21: Error: operand 1 must be an integer or stack pointer register -- `add $384,%r11'
chacha.S: chacha.S:22: Error: operand 1 must be an integer or stack pointer register -- `sub %r11,%rsp'
chacha.S: chacha.S:23: Error: operand 1 must be an integer register -- `mov %rdi,%r8'
chacha.S: chacha.S:24: Error: operand 1 must be an integer register -- `mov %rsi,%rsi'
chacha.S: chacha.S:25: Error: operand 1 must be an integer register -- `mov %rsi,%rdi'
chacha.S: chacha.S:26: Error: operand 1 must be an integer register -- `mov %rdx,%rdx'
chacha.S: chacha.S:27: Error: operand 1 must be an integer or stack pointer register -- `cmp $0,%rdx'
chacha.S: chacha.S:29: Error: unknown mnemonic `jbe' -- `jbe ._done'
chacha.S: chacha.S:31: Error: operand 1 must be an integer register -- `mov $0,%rax'
chacha.S: chacha.S:33: Error: operand 1 must be an integer register -- `mov %rdx,%rcx'
chacha.S: chacha.S:35: Error: unknown mnemonic `rep' -- `rep stosb'
chacha.S: chacha.S:37: Error: operand 1 must be an integer or stack pointer register -- `sub %rdx,%rdi'
chacha.S: chacha.S:39: Error: unknown mnemonic `jmp' -- `jmp ._start'
chacha.S: chacha.S:47: Error: operand 1 must be an integer register -- `mov %rsp,%r11'
chacha.S: chacha.S:48: Error: operand 1 must be an integer or stack pointer register -- `and $31,%r11'
chacha.S: chacha.S:49: Error: operand 1 must be an integer or stack pointer register -- `add $384,%r11'
chacha.S: chacha.S:50: Error: operand 1 must be an integer or stack pointer register -- `sub %r11,%rsp'
chacha.S: chacha.S:52: Error: operand 1 must be an integer register -- `mov %rdi,%r8'
chacha.S: chacha.S:54: Error: operand 1 must be an integer register -- `mov %rsi,%rsi'
chacha.S: chacha.S:56: Error: operand 1 must be an integer register -- `mov %rdx,%rdi'
chacha.S: chacha.S:58: Error: operand 1 must be an integer register -- `mov %rcx,%rdx'
chacha.S: chacha.S:60: Error: operand 1 must be an integer or stack pointer register -- `cmp $0,%rdx'
chacha.S: ...

Compiler output

chacha.c: In file included from chacha.c:94:
chacha.c: ./u4.h:67:14: warning: unused variable 't_5' [-Wunused-variable]
chacha.c:   uint32x4_t t_5;
chacha.c:              ^
chacha.c: ./u4.h:68:14: warning: unused variable 't_6' [-Wunused-variable]
chacha.c:   uint32x4_t t_6;
chacha.c:              ^
chacha.c: ./u4.h:66:14: warning: unused variable 't_4' [-Wunused-variable]
chacha.c:   uint32x4_t t_4;
chacha.c:              ^
chacha.c: ./u4.h:69:14: warning: unused variable 't_7' [-Wunused-variable]
chacha.c:   uint32x4_t t_7;
chacha.c:              ^
chacha.c: ./u4.h:74:14: warning: unused variable 't_12' [-Wunused-variable]
chacha.c:   uint32x4_t t_12;
chacha.c:              ^
chacha.c: ./u4.h:75:14: warning: unused variable 't_13' [-Wunused-variable]
chacha.c:   uint32x4_t t_13;
chacha.c:              ^
chacha.c: ./u4.h:77:14: warning: unused variable 't_15' [-Wunused-variable]
chacha.c:   uint32x4_t t_15;
chacha.c:              ^
chacha.c: ./u4.h:76:14: warning: unused variable 't_14' [-Wunused-variable]
chacha.c:   uint32x4_t t_14;
chacha.c:              ^
chacha.c: ...

Compiler output

chacha.c: In file included from chacha.c:94:
chacha.c: u4.h: In function 'crypto_stream_chacha12_dolbeau_arm_neon_constbranchindex_ECRYPT_encrypt_bytes':
chacha.c: u4.h:77:14: warning: unused variable 't_15' [-Wunused-variable]
chacha.c:    77 |   uint32x4_t t_15;
chacha.c:       |              ^~~~
chacha.c: u4.h:76:14: warning: unused variable 't_14' [-Wunused-variable]
chacha.c:    76 |   uint32x4_t t_14;
chacha.c:       |              ^~~~
chacha.c: u4.h:75:14: warning: unused variable 't_13' [-Wunused-variable]
chacha.c:    75 |   uint32x4_t t_13;
chacha.c:       |              ^~~~
chacha.c: u4.h:74:14: warning: unused variable 't_12' [-Wunused-variable]
chacha.c:    74 |   uint32x4_t t_12;
chacha.c:       |              ^~~~
chacha.c: u4.h:69:14: warning: unused variable 't_7' [-Wunused-variable]
chacha.c:    69 |   uint32x4_t t_7;
chacha.c:       |              ^~~
chacha.c: u4.h:68:14: warning: unused variable 't_6' [-Wunused-variable]
chacha.c:    68 |   uint32x4_t t_6;
chacha.c:       |              ^~~
chacha.c: u4.h:67:14: warning: unused variable 't_5' [-Wunused-variable]
chacha.c:    67 |   uint32x4_t t_5;
chacha.c:       |              ^~~
chacha.c: u4.h:66:14: warning: unused variable 't_4' [-Wunused-variable]
chacha.c:    66 |   uint32x4_t t_4;
chacha.c: ...

Compiler output

chacha.c: In file included from chacha.c:1:
chacha.c: e/chacha.c: In function 'crypto_stream_chacha12_e_merged_constbranchindex_ECRYPT_encrypt_bytes':
chacha.c: e/chacha.c:179:46: warning: 'ctarget' may be used uninitialized in this function [-Wmaybe-uninitialized]
chacha.c:   179 |         for (i = 0;i < bytes;++i) ctarget[i] = c[i];
chacha.c:       |                                   ~~~~~~~~~~~^~~~~~

Compiler output

stream.c: In file included from stream.c:11:
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/immintrin.h:14:2: error: "This header is only meant to be used on x86 and x64 architecture"
stream.c: #error "This header is only meant to be used on x86 and x64 architecture"
stream.c:  ^
stream.c: In file included from stream.c:11:
stream.c: In file included from /usr/lib/llvm-14/lib/clang/14.0.0/include/immintrin.h:17:
stream.c: In file included from /usr/lib/llvm-14/lib/clang/14.0.0/include/x86gprintrin.h:15:
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/hresetintrin.h:42:27: error: invalid input constraint 'a' in asm
stream.c:   __asm__ ("hreset $0" :: "a"(__eax));
stream.c:                           ^
stream.c: In file included from stream.c:11:
stream.c: In file included from /usr/lib/llvm-14/lib/clang/14.0.0/include/immintrin.h:21:
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:14:2: error: "This header is only meant to be used on x86 and x64 architecture"
stream.c: #error "This header is only meant to be used on x86 and x64 architecture"
stream.c:  ^
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:54:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c:     return (__m64)__builtin_ia32_vec_init_v2si(__i, 0);
stream.c:            ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:133:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c:     return (__m64)__builtin_ia32_packsswb((__v4hi)__m1, (__v4hi)__m2);
stream.c:            ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:163:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c:     return (__m64)__builtin_ia32_packssdw((__v2si)__m1, (__v2si)__m2);
stream.c:            ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:193:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c: ...

Compiler output

stream.c: stream.c:11:10: fatal error: immintrin.h: No such file or directory
stream.c:    11 | #include <immintrin.h>
stream.c:       |          ^~~~~~~~~~~~~
stream.c: compilation terminated.

Compiler output

stream.c: In file included from stream.c:8:
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/immintrin.h:14:2: error: "This header is only meant to be used on x86 and x64 architecture"
stream.c: #error "This header is only meant to be used on x86 and x64 architecture"
stream.c:  ^
stream.c: In file included from stream.c:8:
stream.c: In file included from /usr/lib/llvm-14/lib/clang/14.0.0/include/immintrin.h:17:
stream.c: In file included from /usr/lib/llvm-14/lib/clang/14.0.0/include/x86gprintrin.h:15:
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/hresetintrin.h:42:27: error: invalid input constraint 'a' in asm
stream.c:   __asm__ ("hreset $0" :: "a"(__eax));
stream.c:                           ^
stream.c: In file included from stream.c:8:
stream.c: In file included from /usr/lib/llvm-14/lib/clang/14.0.0/include/immintrin.h:21:
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:14:2: error: "This header is only meant to be used on x86 and x64 architecture"
stream.c: #error "This header is only meant to be used on x86 and x64 architecture"
stream.c:  ^
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:54:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c:     return (__m64)__builtin_ia32_vec_init_v2si(__i, 0);
stream.c:            ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:133:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c:     return (__m64)__builtin_ia32_packsswb((__v4hi)__m1, (__v4hi)__m2);
stream.c:            ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:163:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c:     return (__m64)__builtin_ia32_packssdw((__v2si)__m1, (__v2si)__m2);
stream.c:            ^~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~
stream.c: /usr/lib/llvm-14/lib/clang/14.0.0/include/mmintrin.h:193:12: error: invalid conversion between vector type '__m64' (vector of 1 'long long' value) and integer type 'int' of different size
stream.c: ...

Compiler output

stream.c: stream.c:8:10: fatal error: immintrin.h: No such file or directory
stream.c:     8 | #include <immintrin.h>
stream.c:       |          ^~~~~~~~~~~~~
stream.c: compilation terminated.

Compiler output

stream.c: stream.c:80:2: error: -- Implementation supports only machines with neon, altivec or SSE2
stream.c: #error -- Implementation supports only machines with neon, altivec or SSE2
stream.c:  ^
stream.c: stream.c:151:14: warning: implicit declaration of function 'NONCE' is invalid in C99 [-Wimplicit-function-declaration]
stream.c:     vec s3 = NONCE(np);
stream.c:              ^
stream.c: stream.c:151:9: error: initializing 'vec' (vector of 4 'unsigned int' values) with an expression of incompatible type 'int'
stream.c:     vec s3 = NONCE(np);
stream.c:         ^    ~~~~~~~~~
stream.c: stream.c:152:36: error: use of undeclared identifier 'VBPI'
stream.c:     for (iters = 0; iters < inlen/(BPI*64); iters++) {
stream.c:                                    ^
stream.c: stream.c:91:19: note: expanded from macro 'BPI'
stream.c: #define BPI      (VBPI + GPR_TOO)  /* Blocks computed per loop iteration   */
stream.c:                   ^
stream.c: stream.c:152:36: error: use of undeclared identifier 'GPR_TOO'
stream.c: stream.c:91:26: note: expanded from macro 'BPI'
stream.c: #define BPI      (VBPI + GPR_TOO)  /* Blocks computed per loop iteration   */
stream.c:                          ^
stream.c: stream.c:155:19: error: use of undeclared identifier 'ONE'
stream.c:         v7 = v3 + ONE;
stream.c:                   ^
stream.c: stream.c:176:13: warning: implicit declaration of function 'ROTW16' is invalid in C99 [-Wimplicit-function-declaration]
stream.c:             DQROUND_VECTORS(v0,v1,v2,v3)
stream.c:             ^
stream.c: ...

Compiler output

stream.c: stream.c:80:2: error: #error -- Implementation supports only machines with neon, altivec or SSE2
stream.c:    80 | #error -- Implementation supports only machines with neon, altivec or SSE2
stream.c:       |  ^~~~~
stream.c: stream.c: In function 'crypto_stream_chacha12_krovetz_vec128_constbranchindex_xor':
stream.c: stream.c:151:14: warning: implicit declaration of function 'NONCE' [-Wimplicit-function-declaration]
stream.c:   151 |     vec s3 = NONCE(np);
stream.c:       |              ^~~~~
stream.c: stream.c:151:14: error: incompatible types when initializing type 'vec' {aka '__vector(4) unsigned int'} using type 'int'
stream.c: stream.c:91:19: error: 'VBPI' undeclared (first use in this function); did you mean 'BPI'?
stream.c:    91 | #define BPI      (VBPI + GPR_TOO)  /* Blocks computed per loop iteration   */
stream.c:       |                   ^~~~
stream.c: stream.c:152:36: note: in expansion of macro 'BPI'
stream.c:   152 |     for (iters = 0; iters < inlen/(BPI*64); iters++) {
stream.c:       |                                    ^~~
stream.c: stream.c:91:19: note: each undeclared identifier is reported only once for each function it appears in
stream.c:    91 | #define BPI      (VBPI + GPR_TOO)  /* Blocks computed per loop iteration   */
stream.c:       |                   ^~~~
stream.c: stream.c:152:36: note: in expansion of macro 'BPI'
stream.c:   152 |     for (iters = 0; iters < inlen/(BPI*64); iters++) {
stream.c:       |                                    ^~~
stream.c: stream.c:91:26: error: 'GPR_TOO' undeclared (first use in this function)
stream.c:    91 | #define BPI      (VBPI + GPR_TOO)  /* Blocks computed per loop iteration   */
stream.c:       |                          ^~~~~~~
stream.c: stream.c:152:36: note: in expansion of macro 'BPI'
stream.c:   152 |     for (iters = 0; iters < inlen/(BPI*64); iters++) {
stream.c: ...

Passed TIMECOP

TIMECOP iterations: 10