fixes #4477 (libsodium: update to 1.0.20)

7 files changed, 41 insertions, 13 deletions

diff --git a/libs/libsodium/src/crypto_stream/salsa20/stream_salsa20.h b/libs/libsodium/src/crypto_stream/salsa20/stream_salsa20.h
index 0b5971ca48..0b5f3ab184 100644
--- a/libs/libsodium/src/crypto_stream/salsa20/stream_salsa20.h
+++ b/libs/libsodium/src/crypto_stream/salsa20/stream_salsa20.h
@@ -4,6 +4,8 @@
 

 #include <stdint.h>

 

+#include "private/quirks.h"

+

 typedef struct crypto_stream_salsa20_implementation {

     int (*stream)(unsigned char *c, unsigned long long clen,

                   const unsigned char *n, const unsigned char *k);

diff --git a/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6-asm.S b/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6-asm.S
index 9ecea1b088..0406b29da9 100644
--- a/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6-asm.S
+++ b/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6-asm.S
@@ -1,5 +1,8 @@
 #ifdef HAVE_AMD64_ASM

 

+#include "private/asm_cet.h"

+#include "salsa20_xmm6-asm_namespace.h"

+

 .text

 .p2align 5

 

@@ -15,6 +18,8 @@ ASM_HIDE_SYMBOL _stream_salsa20_xmm6
 #endif

 stream_salsa20_xmm6:

 _stream_salsa20_xmm6:

+

+_CET_ENDBR

 mov %rsp,%r11

 and $31,%r11

 add $512,%r11

@@ -56,6 +61,7 @@ ASM_HIDE_SYMBOL _stream_salsa20_xmm6_xor_ic
 stream_salsa20_xmm6_xor_ic:

 _stream_salsa20_xmm6_xor_ic:

 

+_CET_ENDBR

 mov %rsp,%r11

 and $31,%r11

 add $512,%r11

diff --git a/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6-asm_namespace.h b/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6-asm_namespace.h
new file mode 100644
index 0000000000..15c5212ebf
--- /dev/null
+++ b/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6-asm_namespace.h
@@ -0,0 +1,10 @@
+#ifndef salsa20_xmm6_asm_namespace_H
+#define salsa20_xmm6_asm_namespace_H
+
+#define stream_salsa20_xmm6 _sodium_stream_salsa20_xmm6
+#define _stream_salsa20_xmm6 __sodium_stream_salsa20_xmm6
+
+#define stream_salsa20_xmm6_xor_ic _sodium_stream_salsa20_xmm6_xor_ic
+#define _stream_salsa20_xmm6_xor_ic __sodium_stream_salsa20_xmm6_xor_ic
+
+#endif
diff --git a/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6.h b/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6.h
index 3ccbb5e8e6..d88542fd24 100644
--- a/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6.h
+++ b/libs/libsodium/src/crypto_stream/salsa20/xmm6/salsa20_xmm6.h
@@ -3,6 +3,7 @@
 

 #include "../stream_salsa20.h"

 #include "crypto_stream_salsa20.h"

+#include "salsa20_xmm6-asm_namespace.h"

 

 extern struct crypto_stream_salsa20_implementation

     crypto_stream_salsa20_xmm6_implementation;

diff --git a/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-avx2.c b/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-avx2.c
index 95bb63fd13..41cc8a610a 100644
--- a/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-avx2.c
+++ b/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-avx2.c
@@ -5,23 +5,22 @@
 

 #include "crypto_stream_salsa20.h"

 #include "private/common.h"

-#include "private/sse2_64_32.h"

 #include "utils.h"

 

 #if defined(HAVE_AVX2INTRIN_H) && defined(HAVE_EMMINTRIN_H) && \

     defined(HAVE_TMMINTRIN_H) && defined(HAVE_SMMINTRIN_H)

 

-# ifdef __GNUC__

-#  pragma GCC target("sse2")

-#  pragma GCC target("ssse3")

-#  pragma GCC target("sse4.1")

-#  pragma GCC target("avx2")

+# ifdef __clang__

+#  pragma clang attribute push(__attribute__((target("sse2,ssse3,sse4.1,avx2"))), apply_to = function)

+# elif defined(__GNUC__)

+#  pragma GCC target("sse2,ssse3,sse4.1,avx2")

 # endif

 

-#include <emmintrin.h>

-#include <immintrin.h>

-#include <smmintrin.h>

-#include <tmmintrin.h>

+# include <emmintrin.h>

+# include <immintrin.h>

+# include <smmintrin.h>

+# include <tmmintrin.h>

+# include "private/sse2_64_32.h"

 

 # include "../stream_salsa20.h"

 # include "salsa20_xmm6int-avx2.h"

@@ -128,4 +127,8 @@ struct crypto_stream_salsa20_implementation
         SODIUM_C99(.stream_xor_ic =) stream_avx2_xor_ic

     };

 

+#ifdef __clang__

+# pragma clang attribute pop

+#endif

+

 #endif

diff --git a/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-sse2.c b/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-sse2.c
index 41dc8193fc..c3694cd70f 100644
--- a/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-sse2.c
+++ b/libs/libsodium/src/crypto_stream/salsa20/xmm6int/salsa20_xmm6int-sse2.c
@@ -5,15 +5,17 @@
 

 #include "crypto_stream_salsa20.h"

 #include "private/common.h"

-#include "private/sse2_64_32.h"

 #include "utils.h"

 

 #ifdef HAVE_EMMINTRIN_H

 

-# ifdef __GNUC__

+# ifdef __clang__

+#  pragma clang attribute push(__attribute__((target("sse2"))), apply_to = function)

+# elif defined(__GNUC__)

 #  pragma GCC target("sse2")

 # endif

 # include <emmintrin.h>

+# include "private/sse2_64_32.h"

 

 # include "../stream_salsa20.h"

 # include "salsa20_xmm6int-sse2.h"

@@ -119,4 +121,8 @@ struct crypto_stream_salsa20_implementation
         SODIUM_C99(.stream_xor_ic =) stream_sse2_xor_ic

     };

 

+#ifdef __clang__

+# pragma clang attribute pop

+#endif

+

 #endif

diff --git a/libs/libsodium/src/crypto_stream/salsa20/xmm6int/u0.h b/libs/libsodium/src/crypto_stream/salsa20/xmm6int/u0.h
index e2634b4a3e..cce494af6e 100644
--- a/libs/libsodium/src/crypto_stream/salsa20/xmm6int/u0.h
+++ b/libs/libsodium/src/crypto_stream/salsa20/xmm6int/u0.h
@@ -5,7 +5,7 @@ if (bytes > 0) {
     __m128i diag3 = _mm_loadu_si128((const __m128i *) (x + 12));

     __m128i a0, a1, a2, a3, a4, a5, a6, a7;

     __m128i b0, b1, b2, b3, b4, b5, b6, b7;

-    uint8_t partialblock[64];

+    uint8_t partialblock[64] = { 0 };

 

     unsigned int i;