mirror of
https://github.com/cuberite/libdeflate.git
synced 2025-08-04 10:16:44 -04:00
f2c3a5b4e9
* Bring in common headers and program code from xpack project * Move program code to programs/ * Move library code to lib/ * GNU89 and MSVC2010 compatibility * Other changes
62 lines
1.4 KiB
C
62 lines
1.4 KiB
C
/*
|
|
* matchfinder_neon.h - matchfinding routines optimized for ARM NEON (Advanced
|
|
* SIMD) instructions
|
|
*/
|
|
|
|
#include <arm_neon.h>
|
|
|
|
static forceinline bool
|
|
matchfinder_init_neon(mf_pos_t *data, size_t size)
|
|
{
|
|
int16x8_t v, *p;
|
|
size_t n;
|
|
|
|
if (size % sizeof(int16x8_t) * 4)
|
|
return false;
|
|
|
|
STATIC_ASSERT(sizeof(mf_pos_t) == 2);
|
|
v = (int16x8_t) {
|
|
MATCHFINDER_INITVAL, MATCHFINDER_INITVAL, MATCHFINDER_INITVAL,
|
|
MATCHFINDER_INITVAL, MATCHFINDER_INITVAL, MATCHFINDER_INITVAL,
|
|
MATCHFINDER_INITVAL, MATCHFINDER_INITVAL,
|
|
};
|
|
p = (int16x8_t *)data;
|
|
n = size / (sizeof(int16x8_t) * 4);
|
|
do {
|
|
p[0] = v;
|
|
p[1] = v;
|
|
p[2] = v;
|
|
p[3] = v;
|
|
p += 4;
|
|
} while (--n);
|
|
return true;
|
|
}
|
|
|
|
static forceinline bool
|
|
matchfinder_rebase_neon(mf_pos_t *data, size_t size)
|
|
{
|
|
int16x8_t v, *p;
|
|
size_t n;
|
|
|
|
if ((size % sizeof(int16x8_t) * 4 != 0))
|
|
return false;
|
|
|
|
STATIC_ASSERT(sizeof(mf_pos_t) == 2);
|
|
v = (int16x8_t) {
|
|
(u16)-MATCHFINDER_WINDOW_SIZE, (u16)-MATCHFINDER_WINDOW_SIZE,
|
|
(u16)-MATCHFINDER_WINDOW_SIZE, (u16)-MATCHFINDER_WINDOW_SIZE,
|
|
(u16)-MATCHFINDER_WINDOW_SIZE, (u16)-MATCHFINDER_WINDOW_SIZE,
|
|
(u16)-MATCHFINDER_WINDOW_SIZE, (u16)-MATCHFINDER_WINDOW_SIZE,
|
|
};
|
|
p = (int16x8_t *)data;
|
|
n = size / (sizeof(int16x8_t) * 4);
|
|
do {
|
|
p[0] = vqaddq_s16(p[0], v);
|
|
p[1] = vqaddq_s16(p[1], v);
|
|
p[2] = vqaddq_s16(p[2], v);
|
|
p[3] = vqaddq_s16(p[3], v);
|
|
p += 4;
|
|
} while (--n);
|
|
return true;
|
|
}
|