avx2: apply BASE64_FORCE_INLINE macro

aklomp · Jan 13, 2024 · 08fa9d8 · 08fa9d8
1 parent c19f146
commit 08fa9d8
Show file tree

Hide file tree

Showing 6 changed files with 9 additions and 9 deletions.
diff --git a/lib/arch/avx2/dec_loop.c b/lib/arch/avx2/dec_loop.c
@@ -1,4 +1,4 @@
-static inline int
+BASE64_FORCE_INLINE int
 dec_loop_avx2_inner (const uint8_t **s, uint8_t **o, size_t *rounds)
 {
 	const __m256i lut_lo = _mm256_setr_epi8(
@@ -53,7 +53,7 @@ dec_loop_avx2_inner (const uint8_t **s, uint8_t **o, size_t *rounds)
 	return 1;
 }
 
-static inline void
+BASE64_FORCE_INLINE void
 dec_loop_avx2 (const uint8_t **s, size_t *slen, uint8_t **o, size_t *olen)
 {
 	if (*slen < 45) {

diff --git a/lib/arch/avx2/dec_reshuffle.c b/lib/arch/avx2/dec_reshuffle.c
@@ -1,4 +1,4 @@
-static inline __m256i
+BASE64_FORCE_INLINE __m256i
 dec_reshuffle (const __m256i in)
 {
 	// in, lower lane, bits, upper case are most significant bits, lower

diff --git a/lib/arch/avx2/enc_loop.c b/lib/arch/avx2/enc_loop.c
@@ -1,4 +1,4 @@
-static inline void
+BASE64_FORCE_INLINE void
 enc_loop_avx2_inner_first (const uint8_t **s, uint8_t **o)
 {
 	// First load is done at s - 0 to not get a segfault:
@@ -17,7 +17,7 @@ enc_loop_avx2_inner_first (const uint8_t **s, uint8_t **o)
 	*o += 32;
 }
 
-static inline void
+BASE64_FORCE_INLINE void
 enc_loop_avx2_inner (const uint8_t **s, uint8_t **o)
 {
 	// Load input:
@@ -32,7 +32,7 @@ enc_loop_avx2_inner (const uint8_t **s, uint8_t **o)
 	*o += 32;
 }
 
-static inline void
+BASE64_FORCE_INLINE void
 enc_loop_avx2 (const uint8_t **s, size_t *slen, uint8_t **o, size_t *olen)
 {
 	if (*slen < 32) {

diff --git a/lib/arch/avx2/enc_loop_asm.c b/lib/arch/avx2/enc_loop_asm.c
@@ -119,7 +119,7 @@
 #pragma GCC diagnostic push
 #pragma GCC diagnostic ignored "-Woverlength-strings"
 
-static inline void
+BASE64_FORCE_INLINE void
 enc_loop_avx2 (const uint8_t **s, size_t *slen, uint8_t **o, size_t *olen)
 {
 	// For a clearer explanation of the algorithm used by this function,

diff --git a/lib/arch/avx2/enc_reshuffle.c b/lib/arch/avx2/enc_reshuffle.c
@@ -1,4 +1,4 @@
-static inline __m256i
+BASE64_FORCE_INLINE __m256i
 enc_reshuffle (const __m256i input)
 {
 	// Translation of the SSSE3 reshuffling algorithm to AVX2. This one

diff --git a/lib/arch/avx2/enc_translate.c b/lib/arch/avx2/enc_translate.c
@@ -1,4 +1,4 @@
-static inline __m256i
+BASE64_FORCE_INLINE __m256i
 enc_translate (const __m256i in)
 {
 	// A lookup table containing the absolute offsets for all ranges: