You cannot select more than 25 topics
Topics must start with a letter or number, can include dashes ('-') and can be up to 35 characters long.
79 lines
2.1 KiB
C++
79 lines
2.1 KiB
C++
// SPDX-License-Identifier: GPL-2.0-or-later
|
|
// Copyright The Music Player Daemon Project
|
|
|
|
#ifndef MPD_PCM_NEON_HXX
|
|
#define MPD_PCM_NEON_HXX
|
|
|
|
#include "Traits.hxx"
|
|
|
|
#include <arm_neon.h>
|
|
|
|
/**
|
|
* Call a NEON intrinsic for each element in the vector.
|
|
*
|
|
* @param func the NEON intrinsic
|
|
* @param result the vector variable that gets assigned the result
|
|
* @param vector the input vector
|
|
*/
|
|
#define neon_x4_u(func, result, vector) do { \
|
|
result.val[0] = func(vector.val[0]); \
|
|
result.val[1] = func(vector.val[1]); \
|
|
result.val[2] = func(vector.val[2]); \
|
|
result.val[3] = func(vector.val[3]); \
|
|
} while (0)
|
|
|
|
/**
|
|
* Call a NEON intrinsic for each element in the vector.
|
|
*
|
|
* @param func the NEON intrinsic
|
|
* @param result the vector variable that gets assigned the result
|
|
* @param vector the input vector
|
|
*/
|
|
#define neon_x4_b(func, result, vector, ...) do { \
|
|
result.val[0] = func(vector.val[0], __VA_ARGS__); \
|
|
result.val[1] = func(vector.val[1], __VA_ARGS__); \
|
|
result.val[2] = func(vector.val[2], __VA_ARGS__); \
|
|
result.val[3] = func(vector.val[3], __VA_ARGS__); \
|
|
} while (0)
|
|
|
|
/**
|
|
* Convert floating point samples to 16 bit signed integer using ARM NEON.
|
|
*/
|
|
struct NeonFloatTo16 {
|
|
static constexpr SampleFormat src_format = SampleFormat::FLOAT;
|
|
static constexpr SampleFormat dst_format = SampleFormat::S16;
|
|
typedef SampleTraits<src_format> SrcTraits;
|
|
typedef SampleTraits<dst_format> DstTraits;
|
|
|
|
typedef typename SrcTraits::value_type SV;
|
|
typedef typename DstTraits::value_type DV;
|
|
|
|
static constexpr size_t BLOCK_SIZE = 16;
|
|
|
|
void Convert(int16_t *dst, const float *src,
|
|
const size_t n) const noexcept {
|
|
for (unsigned i = 0; i < n / BLOCK_SIZE;
|
|
++i, src += BLOCK_SIZE, dst += BLOCK_SIZE) {
|
|
/* load 16 float samples into 4 quad
|
|
registers */
|
|
float32x4x4_t value = vld4q_f32(src);
|
|
|
|
/* convert to 32 bit integer */
|
|
int32x4x4_t ivalue;
|
|
neon_x4_b(vcvtq_n_s32_f32, ivalue, value,
|
|
30);
|
|
|
|
/* convert to 16 bit integer with saturation
|
|
and rounding */
|
|
int16x4x4_t nvalue;
|
|
neon_x4_b(vqrshrn_n_s32, nvalue, ivalue,
|
|
30 - DstTraits::BITS + 1);
|
|
|
|
/* store result */
|
|
vst4_s16(dst, nvalue);
|
|
}
|
|
}
|
|
};
|
|
|
|
#endif
|