Skip to content

Commit

Permalink
Remove broken volk_16i_max_star_16i_neon protokernel
Browse files Browse the repository at this point in the history
Signed-off-by: Clayton Smith <[email protected]>
  • Loading branch information
argilo committed Nov 4, 2023
1 parent d5b317c commit afbc10e
Showing 1 changed file with 0 additions and 41 deletions.
41 changes: 0 additions & 41 deletions kernels/volk/volk_16i_max_star_16i.h
Original file line number Diff line number Diff line change
Expand Up @@ -107,47 +107,6 @@ volk_16i_max_star_16i_a_ssse3(short* target, short* src0, unsigned int num_point

#endif /*LV_HAVE_SSSE3*/

#ifdef LV_HAVE_NEON
#include <arm_neon.h>

static inline void
volk_16i_max_star_16i_neon(short* target, short* src0, unsigned int num_points)
{
const unsigned int eighth_points = num_points / 8;
unsigned number;
int16x8_t input_vec;
int16x8_t diff, zeros;
uint16x8_t comp1, comp2;
zeros = vdupq_n_s16(0);

int16x8x2_t tmpvec;

int16x8_t candidate_vec = vld1q_dup_s16(src0);
short candidate;
++src0;

for (number = 0; number < eighth_points; ++number) {
input_vec = vld1q_s16(src0);
__VOLK_PREFETCH(src0 + 16);
diff = vsubq_s16(candidate_vec, input_vec);
comp1 = vcgeq_s16(diff, zeros);
comp2 = vcltq_s16(diff, zeros);

tmpvec.val[0] = vandq_s16(candidate_vec, (int16x8_t)comp1);
tmpvec.val[1] = vandq_s16(input_vec, (int16x8_t)comp2);

candidate_vec = vaddq_s16(tmpvec.val[0], tmpvec.val[1]);
src0 += 8;
}
vst1q_s16(&candidate, candidate_vec);

for (number = 0; number < num_points % 8; number++) {
candidate = ((int16_t)(candidate - src0[number]) > 0) ? candidate : src0[number];
}
target[0] = candidate;
}
#endif /*LV_HAVE_NEON*/

#ifdef LV_HAVE_GENERIC

static inline void
Expand Down

0 comments on commit afbc10e

Please sign in to comment.