facebook/zstd
1
0
Fork 0
Code Issues Pull Requests Packages Projects Releases Wiki Activity

Add ZSTD_NO_INTRINSICS macro to avoid explicit intrinsics

Browse Source
This commit is contained in:
Nick Terrell 2020-08-14 12:41:28 -07:00
parent f91ed5c766
commit e975de289c
2 changed files with 9 additions and 7 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

10
lib/common/bitstream.h
View File

@ -35,10 +35,12 @@ extern "C" {
/*========================================= /*=========================================
* Target specific * Target specific
=========================================*/ =========================================*/
#if defined(__BMI__) && defined(__GNUC__) #ifndef ZSTD_NO_INTRINSICS
# include <immintrin.h> /* support for bextr (experimental) */ # if defined(__BMI__) && defined(__GNUC__)
#elif defined(__ICCARM__) # include <immintrin.h> /* support for bextr (experimental) */
# include <intrinsics.h> # elif defined(__ICCARM__)
# include <intrinsics.h>
# endif
#endif #endif
#define STREAM_ACCUMULATOR_MIN_32 25 #define STREAM_ACCUMULATOR_MIN_32 25

6
lib/common/zstd_internal.h
View File

@ -19,7 +19,7 @@
/*-************************************* /*-*************************************
* Dependencies * Dependencies
***************************************/ ***************************************/
#ifdef __aarch64__ #if !defined(ZSTD_NO_INTRINSICS) && defined(__aarch64__)
#include <arm_neon.h> #include <arm_neon.h>
#endif #endif
#include "compiler.h" #include "compiler.h"
@ -228,7 +228,7 @@ static const U32 OF_defaultNormLog = OF_DEFAULTNORMLOG;
* Shared functions to include for inlining * Shared functions to include for inlining
*********************************************/ *********************************************/
static void ZSTD_copy8(void* dst, const void* src) { static void ZSTD_copy8(void* dst, const void* src) {
#ifdef __aarch64__ #if !defined(ZSTD_NO_INTRINSICS) && defined(__aarch64__)
vst1_u8((uint8_t*)dst, vld1_u8((const uint8_t*)src)); vst1_u8((uint8_t*)dst, vld1_u8((const uint8_t*)src));
#else #else
ZSTD_memcpy(dst, src, 8); ZSTD_memcpy(dst, src, 8);
@ -237,7 +237,7 @@ static void ZSTD_copy8(void* dst, const void* src) {
#define COPY8(d,s) { ZSTD_copy8(d,s); d+=8; s+=8; } #define COPY8(d,s) { ZSTD_copy8(d,s); d+=8; s+=8; }
static void ZSTD_copy16(void* dst, const void* src) { static void ZSTD_copy16(void* dst, const void* src) {
#ifdef __aarch64__ #if !defined(ZSTD_NO_INTRINSICS) && defined(__aarch64__)
vst1q_u8((uint8_t*)dst, vld1q_u8((const uint8_t*)src)); vst1q_u8((uint8_t*)dst, vld1q_u8((const uint8_t*)src));
#else #else
ZSTD_memcpy(dst, src, 16); ZSTD_memcpy(dst, src, 16);