]> git.proxmox.com Git - mirror_ubuntu-kernels.git/commit
UBUNTU: SAUCE: apply a workaround to re-enable CONFIG_CRYPTO_AEGIS128_SIMD
authorAndrea Righi <andrea.righi@canonical.com>
Thu, 30 Jul 2020 15:31:37 +0000 (17:31 +0200)
committerAndrea Righi <andrea.righi@canonical.com>
Thu, 9 Mar 2023 14:57:22 +0000 (15:57 +0100)
commitd5f3e712a836e7aac6bf78004b595ecf43b59387
tree28d9423bb2d240d1aa1cde86c08fc6765a70ef63
parentc8ea033ffdbad26c981406e441bf9d72147800b9
UBUNTU: SAUCE: apply a workaround to re-enable CONFIG_CRYPTO_AEGIS128_SIMD

After the update to gcc 10 we started to experience the following build
errors on ARM:

  crypto/aegis128-neon-inner.c: In function 'crypto_aegis128_init_neon':
  crypto/aegis128-neon-inner.c:151:3: error: incompatible types when initializing type 'unsigned char' using type 'uint8x16_t'
    151 |   k ^ vld1q_u8(const0),
|   ^
  crypto/aegis128-neon-inner.c:152:3: error: incompatible types when initializing type 'unsigned char' using type 'uint8x16_t'
    152 |   k ^ vld1q_u8(const1),
|   ^

This seems to be a gcc bug:
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=96377

The workaround (suggested in the bug report) is to enforce a cast to
uint8x16_t.

Apply the workaround so that we can re-enable the driver disabled by
7c950e057db6 ("UBUNTU: [Config] disable CONFIG_CRYPTO_AEGIS128_SIMD").

Signed-off-by: Andrea Righi <andrea.righi@canonical.com>
crypto/aegis128-neon-inner.c