Loading...
Searching...
No Matches
volk_32f_s32f_calc_spectral_noise_floor_32f.h
Go to the documentation of this file.
/* -*- c++ -*- */
/*
* Copyright 2012, 2014 Free Software Foundation, Inc.
*
* This file is part of VOLK
*
* SPDX-License-Identifier: LGPL-3.0-or-later
*/
#ifndef INCLUDED_volk_32f_s32f_calc_spectral_noise_floor_32f_a_H
#define INCLUDED_volk_32f_s32f_calc_spectral_noise_floor_32f_a_H
#include <inttypes.h>
#include <stdio.h>
#include <volk/volk_common.h>
#include <volk/volk_32f_accumulator_s32f.h>
#ifdef LV_HAVE_AVX
#include <immintrin.h>
static inline void
volk_32f_s32f_calc_spectral_noise_floor_32f_a_avx(float* noiseFloorAmplitude,
const float* realDataPoints,
const float spectralExclusionValue,
const unsigned int num_points)
{
unsigned int number = 0;
const unsigned int eighthPoints = num_points / 8;
const float* dataPointsPtr = realDataPoints;
__VOLK_ATTR_ALIGNED(32) float avgPointsVector[8];
__m256 dataPointsVal;
__m256 avgPointsVal = _mm256_setzero_ps();
// Calculate the sum (for mean) for all points
for (; number < eighthPoints; number++) {
dataPointsVal = _mm256_load_ps(dataPointsPtr);
dataPointsPtr += 8;
avgPointsVal = _mm256_add_ps(avgPointsVal, dataPointsVal);
}
_mm256_store_ps(avgPointsVector, avgPointsVal);
float sumMean = 0.0;
sumMean += avgPointsVector[0];
sumMean += avgPointsVector[1];
sumMean += avgPointsVector[2];
sumMean += avgPointsVector[3];
sumMean += avgPointsVector[4];
sumMean += avgPointsVector[5];
sumMean += avgPointsVector[6];
sumMean += avgPointsVector[7];
number = eighthPoints * 8;
for (; number < num_points; number++) {
sumMean += realDataPoints[number];
}
// calculate the spectral mean
// +20 because for the comparison below we only want to throw out bins
// that are significantly higher (and would, thus, affect the mean more
const float meanAmplitude = (sumMean / ((float)num_points)) + spectralExclusionValue;
dataPointsPtr = realDataPoints; // Reset the dataPointsPtr
__m256 vMeanAmplitudeVector = _mm256_set1_ps(meanAmplitude);
__m256 vOnesVector = _mm256_set1_ps(1.0);
__m256 vValidBinCount = _mm256_setzero_ps();
avgPointsVal = _mm256_setzero_ps();
__m256 compareMask;
number = 0;
// Calculate the sum (for mean) for any points which do NOT exceed the mean amplitude
for (; number < eighthPoints; number++) {
dataPointsVal = _mm256_load_ps(dataPointsPtr);
dataPointsPtr += 8;
// Identify which items do not exceed the mean amplitude
compareMask = _mm256_cmp_ps(dataPointsVal, vMeanAmplitudeVector, _CMP_LE_OQ);
// Mask off the items that exceed the mean amplitude and add the avg Points that
// do not exceed the mean amplitude
avgPointsVal =
_mm256_add_ps(avgPointsVal, _mm256_and_ps(compareMask, dataPointsVal));
// Count the number of bins which do not exceed the mean amplitude
vValidBinCount =
_mm256_add_ps(vValidBinCount, _mm256_and_ps(compareMask, vOnesVector));
}
// Calculate the mean from the remaining data points
_mm256_store_ps(avgPointsVector, avgPointsVal);
sumMean = 0.0;
sumMean += avgPointsVector[0];
sumMean += avgPointsVector[1];
sumMean += avgPointsVector[2];
sumMean += avgPointsVector[3];
sumMean += avgPointsVector[4];
sumMean += avgPointsVector[5];
sumMean += avgPointsVector[6];
sumMean += avgPointsVector[7];
// Calculate the number of valid bins from the remaining count
__VOLK_ATTR_ALIGNED(32) float validBinCountVector[8];
_mm256_store_ps(validBinCountVector, vValidBinCount);
float validBinCount = 0;
validBinCount += validBinCountVector[0];
validBinCount += validBinCountVector[1];
validBinCount += validBinCountVector[2];
validBinCount += validBinCountVector[3];
validBinCount += validBinCountVector[4];
validBinCount += validBinCountVector[5];
validBinCount += validBinCountVector[6];
validBinCount += validBinCountVector[7];
number = eighthPoints * 8;
for (; number < num_points; number++) {
if (realDataPoints[number] <= meanAmplitude) {
sumMean += realDataPoints[number];
validBinCount += 1.0;
}
}
float localNoiseFloorAmplitude = 0;
if (validBinCount > 0.0) {
localNoiseFloorAmplitude = sumMean / validBinCount;
} else {
localNoiseFloorAmplitude =
meanAmplitude; // For the odd case that all the amplitudes are equal...
}
*noiseFloorAmplitude = localNoiseFloorAmplitude;
}
#endif /* LV_HAVE_AVX */
#ifdef LV_HAVE_SSE
#include <xmmintrin.h>
static inline void
volk_32f_s32f_calc_spectral_noise_floor_32f_a_sse(float* noiseFloorAmplitude,
const float* realDataPoints,
const float spectralExclusionValue,
const unsigned int num_points)
{
unsigned int number = 0;
const unsigned int quarterPoints = num_points / 4;
const float* dataPointsPtr = realDataPoints;
__VOLK_ATTR_ALIGNED(16) float avgPointsVector[4];
__m128 dataPointsVal;
__m128 avgPointsVal = _mm_setzero_ps();
// Calculate the sum (for mean) for all points
for (; number < quarterPoints; number++) {
dataPointsVal = _mm_load_ps(dataPointsPtr);
dataPointsPtr += 4;
avgPointsVal = _mm_add_ps(avgPointsVal, dataPointsVal);
}
_mm_store_ps(avgPointsVector, avgPointsVal);
float sumMean = 0.0;
sumMean += avgPointsVector[0];
sumMean += avgPointsVector[1];
sumMean += avgPointsVector[2];
sumMean += avgPointsVector[3];
number = quarterPoints * 4;
for (; number < num_points; number++) {
sumMean += realDataPoints[number];
}
// calculate the spectral mean
// +20 because for the comparison below we only want to throw out bins
// that are significantly higher (and would, thus, affect the mean more
const float meanAmplitude = (sumMean / ((float)num_points)) + spectralExclusionValue;
dataPointsPtr = realDataPoints; // Reset the dataPointsPtr
__m128 vMeanAmplitudeVector = _mm_set_ps1(meanAmplitude);
__m128 vOnesVector = _mm_set_ps1(1.0);
__m128 vValidBinCount = _mm_setzero_ps();
avgPointsVal = _mm_setzero_ps();
__m128 compareMask;
number = 0;
// Calculate the sum (for mean) for any points which do NOT exceed the mean amplitude
for (; number < quarterPoints; number++) {
dataPointsVal = _mm_load_ps(dataPointsPtr);
dataPointsPtr += 4;
// Identify which items do not exceed the mean amplitude
compareMask = _mm_cmple_ps(dataPointsVal, vMeanAmplitudeVector);
// Mask off the items that exceed the mean amplitude and add the avg Points that
// do not exceed the mean amplitude
avgPointsVal = _mm_add_ps(avgPointsVal, _mm_and_ps(compareMask, dataPointsVal));
// Count the number of bins which do not exceed the mean amplitude
vValidBinCount = _mm_add_ps(vValidBinCount, _mm_and_ps(compareMask, vOnesVector));
}
// Calculate the mean from the remaining data points
_mm_store_ps(avgPointsVector, avgPointsVal);
sumMean = 0.0;
sumMean += avgPointsVector[0];
sumMean += avgPointsVector[1];
sumMean += avgPointsVector[2];
sumMean += avgPointsVector[3];
// Calculate the number of valid bins from the remaining count
__VOLK_ATTR_ALIGNED(16) float validBinCountVector[4];
_mm_store_ps(validBinCountVector, vValidBinCount);
float validBinCount = 0;
validBinCount += validBinCountVector[0];
validBinCount += validBinCountVector[1];
validBinCount += validBinCountVector[2];
validBinCount += validBinCountVector[3];
number = quarterPoints * 4;
for (; number < num_points; number++) {
if (realDataPoints[number] <= meanAmplitude) {
sumMean += realDataPoints[number];
validBinCount += 1.0;
}
}
float localNoiseFloorAmplitude = 0;
if (validBinCount > 0.0) {
localNoiseFloorAmplitude = sumMean / validBinCount;
} else {
localNoiseFloorAmplitude =
meanAmplitude; // For the odd case that all the amplitudes are equal...
}
*noiseFloorAmplitude = localNoiseFloorAmplitude;
}
#endif /* LV_HAVE_SSE */
#ifdef LV_HAVE_GENERIC
static inline void
volk_32f_s32f_calc_spectral_noise_floor_32f_generic(float* noiseFloorAmplitude,
const float* realDataPoints,
const float spectralExclusionValue,
const unsigned int num_points)
{
float sumMean = 0.0;
unsigned int number;
// find the sum (for mean), etc
for (number = 0; number < num_points; number++) {
// sum (for mean)
sumMean += realDataPoints[number];
}
// calculate the spectral mean
// +20 because for the comparison below we only want to throw out bins
// that are significantly higher (and would, thus, affect the mean more)
const float meanAmplitude = (sumMean / num_points) + spectralExclusionValue;
// now throw out any bins higher than the mean
sumMean = 0.0;
unsigned int newNumDataPoints = num_points;
for (number = 0; number < num_points; number++) {
if (realDataPoints[number] <= meanAmplitude)
sumMean += realDataPoints[number];
else
newNumDataPoints--;
}
float localNoiseFloorAmplitude = 0.0;
if (newNumDataPoints == 0) // in the odd case that all
localNoiseFloorAmplitude = meanAmplitude; // amplitudes are equal!
else
localNoiseFloorAmplitude = sumMean / ((float)newNumDataPoints);
*noiseFloorAmplitude = localNoiseFloorAmplitude;
}
#endif /* LV_HAVE_GENERIC */
#ifdef LV_HAVE_NEON
#include <arm_neon.h>
static inline void
volk_32f_s32f_calc_spectral_noise_floor_32f_neon(float* noiseFloorAmplitude,
const float* realDataPoints,
const float spectralExclusionValue,
const unsigned int num_points)
{
unsigned int number = 0;
const unsigned int quarterPoints = num_points / 4;
const float* dataPointsPtr = realDataPoints;
float32x4_t avgPointsVal = vdupq_n_f32(0.0f);
// Calculate the sum (for mean) for all points
for (; number < quarterPoints; number++) {
float32x4_t dataPointsVal = vld1q_f32(dataPointsPtr);
dataPointsPtr += 4;
avgPointsVal = vaddq_f32(avgPointsVal, dataPointsVal);
}
// Horizontal sum
float32x2_t sum2 = vadd_f32(vget_low_f32(avgPointsVal), vget_high_f32(avgPointsVal));
float sumMean = vget_lane_f32(vpadd_f32(sum2, sum2), 0);
number = quarterPoints * 4;
for (; number < num_points; number++) {
sumMean += realDataPoints[number];
}
// calculate the spectral mean
const float meanAmplitude = (sumMean / ((float)num_points)) + spectralExclusionValue;
dataPointsPtr = realDataPoints;
float32x4_t vMeanAmplitudeVector = vdupq_n_f32(meanAmplitude);
float32x4_t vOnesVector = vdupq_n_f32(1.0f);
float32x4_t vValidBinCount = vdupq_n_f32(0.0f);
avgPointsVal = vdupq_n_f32(0.0f);
number = 0;
// Calculate the sum (for mean) for any points which do NOT exceed the mean amplitude
for (; number < quarterPoints; number++) {
float32x4_t dataPointsVal = vld1q_f32(dataPointsPtr);
dataPointsPtr += 4;
// Identify which items do not exceed the mean amplitude
uint32x4_t compareMask = vcleq_f32(dataPointsVal, vMeanAmplitudeVector);
// Mask off the items that exceed the mean amplitude
float32x4_t maskedData = vbslq_f32(compareMask, dataPointsVal, vdupq_n_f32(0.0f));
avgPointsVal = vaddq_f32(avgPointsVal, maskedData);
// Count the number of bins which do not exceed the mean amplitude
float32x4_t maskedOnes = vbslq_f32(compareMask, vOnesVector, vdupq_n_f32(0.0f));
vValidBinCount = vaddq_f32(vValidBinCount, maskedOnes);
}
// Horizontal sums
sum2 = vadd_f32(vget_low_f32(avgPointsVal), vget_high_f32(avgPointsVal));
sumMean = vget_lane_f32(vpadd_f32(sum2, sum2), 0);
float32x2_t cnt2 =
vadd_f32(vget_low_f32(vValidBinCount), vget_high_f32(vValidBinCount));
float validBinCount = vget_lane_f32(vpadd_f32(cnt2, cnt2), 0);
number = quarterPoints * 4;
for (; number < num_points; number++) {
if (realDataPoints[number] <= meanAmplitude) {
sumMean += realDataPoints[number];
validBinCount += 1.0f;
}
}
float localNoiseFloorAmplitude = 0;
if (validBinCount > 0.0f) {
localNoiseFloorAmplitude = sumMean / validBinCount;
} else {
localNoiseFloorAmplitude = meanAmplitude;
}
*noiseFloorAmplitude = localNoiseFloorAmplitude;
}
#endif /* LV_HAVE_NEON */
#ifdef LV_HAVE_NEONV8
#include <arm_neon.h>
static inline void
volk_32f_s32f_calc_spectral_noise_floor_32f_neonv8(float* noiseFloorAmplitude,
const float* realDataPoints,
const float spectralExclusionValue,
const unsigned int num_points)
{
unsigned int number = 0;
const unsigned int eighthPoints = num_points / 8;
const float* dataPointsPtr = realDataPoints;
float32x4_t avgPointsVal0 = vdupq_n_f32(0.0f);
float32x4_t avgPointsVal1 = vdupq_n_f32(0.0f);
// Calculate the sum (for mean) for all points
for (; number < eighthPoints; number++) {
__VOLK_PREFETCH(dataPointsPtr + 16);
float32x4_t dataPointsVal0 = vld1q_f32(dataPointsPtr);
float32x4_t dataPointsVal1 = vld1q_f32(dataPointsPtr + 4);
dataPointsPtr += 8;
avgPointsVal0 = vaddq_f32(avgPointsVal0, dataPointsVal0);
avgPointsVal1 = vaddq_f32(avgPointsVal1, dataPointsVal1);
}
// Combine and horizontal sum using vaddvq_f32
float32x4_t avgPointsVal = vaddq_f32(avgPointsVal0, avgPointsVal1);
float sumMean = vaddvq_f32(avgPointsVal);
number = eighthPoints * 8;
for (; number < num_points; number++) {
sumMean += realDataPoints[number];
}
// calculate the spectral mean
const float meanAmplitude = (sumMean / ((float)num_points)) + spectralExclusionValue;
dataPointsPtr = realDataPoints;
float32x4_t vMeanAmplitudeVector = vdupq_n_f32(meanAmplitude);
float32x4_t vOnesVector = vdupq_n_f32(1.0f);
float32x4_t vValidBinCount0 = vdupq_n_f32(0.0f);
float32x4_t vValidBinCount1 = vdupq_n_f32(0.0f);
avgPointsVal0 = vdupq_n_f32(0.0f);
avgPointsVal1 = vdupq_n_f32(0.0f);
number = 0;
// Calculate the sum (for mean) for any points which do NOT exceed the mean amplitude
for (; number < eighthPoints; number++) {
__VOLK_PREFETCH(dataPointsPtr + 16);
float32x4_t dataPointsVal0 = vld1q_f32(dataPointsPtr);
float32x4_t dataPointsVal1 = vld1q_f32(dataPointsPtr + 4);
dataPointsPtr += 8;
// Identify which items do not exceed the mean amplitude
uint32x4_t compareMask0 = vcleq_f32(dataPointsVal0, vMeanAmplitudeVector);
uint32x4_t compareMask1 = vcleq_f32(dataPointsVal1, vMeanAmplitudeVector);
// Mask off the items that exceed the mean amplitude
float32x4_t maskedData0 =
vbslq_f32(compareMask0, dataPointsVal0, vdupq_n_f32(0.0f));
float32x4_t maskedData1 =
vbslq_f32(compareMask1, dataPointsVal1, vdupq_n_f32(0.0f));
avgPointsVal0 = vaddq_f32(avgPointsVal0, maskedData0);
avgPointsVal1 = vaddq_f32(avgPointsVal1, maskedData1);
// Count the number of bins which do not exceed the mean amplitude
float32x4_t maskedOnes0 = vbslq_f32(compareMask0, vOnesVector, vdupq_n_f32(0.0f));
float32x4_t maskedOnes1 = vbslq_f32(compareMask1, vOnesVector, vdupq_n_f32(0.0f));
vValidBinCount0 = vaddq_f32(vValidBinCount0, maskedOnes0);
vValidBinCount1 = vaddq_f32(vValidBinCount1, maskedOnes1);
}
// Combine and horizontal sums
avgPointsVal = vaddq_f32(avgPointsVal0, avgPointsVal1);
sumMean = vaddvq_f32(avgPointsVal);
float32x4_t vValidBinCount = vaddq_f32(vValidBinCount0, vValidBinCount1);
float validBinCount = vaddvq_f32(vValidBinCount);
number = eighthPoints * 8;
for (; number < num_points; number++) {
if (realDataPoints[number] <= meanAmplitude) {
sumMean += realDataPoints[number];
validBinCount += 1.0f;
}
}
float localNoiseFloorAmplitude = 0;
if (validBinCount > 0.0f) {
localNoiseFloorAmplitude = sumMean / validBinCount;
} else {
localNoiseFloorAmplitude = meanAmplitude;
}
*noiseFloorAmplitude = localNoiseFloorAmplitude;
}
#endif /* LV_HAVE_NEONV8 */
#endif /* INCLUDED_volk_32f_s32f_calc_spectral_noise_floor_32f_a_H */
#ifndef INCLUDED_volk_32f_s32f_calc_spectral_noise_floor_32f_u_H
#define INCLUDED_volk_32f_s32f_calc_spectral_noise_floor_32f_u_H
#include <inttypes.h>
#include <stdio.h>
#include <volk/volk_common.h>
#ifdef LV_HAVE_AVX
#include <immintrin.h>
static inline void
volk_32f_s32f_calc_spectral_noise_floor_32f_u_avx(float* noiseFloorAmplitude,
const float* realDataPoints,
const float spectralExclusionValue,
const unsigned int num_points)
{
unsigned int number = 0;
const unsigned int eighthPoints = num_points / 8;
const float* dataPointsPtr = realDataPoints;
__VOLK_ATTR_ALIGNED(16) float avgPointsVector[8];
__m256 dataPointsVal;
__m256 avgPointsVal = _mm256_setzero_ps();
// Calculate the sum (for mean) for all points
for (; number < eighthPoints; number++) {
dataPointsVal = _mm256_loadu_ps(dataPointsPtr);
dataPointsPtr += 8;
avgPointsVal = _mm256_add_ps(avgPointsVal, dataPointsVal);
}
_mm256_storeu_ps(avgPointsVector, avgPointsVal);
float sumMean = 0.0;
sumMean += avgPointsVector[0];
sumMean += avgPointsVector[1];
sumMean += avgPointsVector[2];
sumMean += avgPointsVector[3];
sumMean += avgPointsVector[4];
sumMean += avgPointsVector[5];
sumMean += avgPointsVector[6];
sumMean += avgPointsVector[7];
number = eighthPoints * 8;
for (; number < num_points; number++) {
sumMean += realDataPoints[number];
}
// calculate the spectral mean
// +20 because for the comparison below we only want to throw out bins
// that are significantly higher (and would, thus, affect the mean more
const float meanAmplitude = (sumMean / ((float)num_points)) + spectralExclusionValue;
dataPointsPtr = realDataPoints; // Reset the dataPointsPtr
__m256 vMeanAmplitudeVector = _mm256_set1_ps(meanAmplitude);
__m256 vOnesVector = _mm256_set1_ps(1.0);
__m256 vValidBinCount = _mm256_setzero_ps();
avgPointsVal = _mm256_setzero_ps();
__m256 compareMask;
number = 0;
// Calculate the sum (for mean) for any points which do NOT exceed the mean amplitude
for (; number < eighthPoints; number++) {
dataPointsVal = _mm256_loadu_ps(dataPointsPtr);
dataPointsPtr += 8;
// Identify which items do not exceed the mean amplitude
compareMask = _mm256_cmp_ps(dataPointsVal, vMeanAmplitudeVector, _CMP_LE_OQ);
// Mask off the items that exceed the mean amplitude and add the avg Points that
// do not exceed the mean amplitude
avgPointsVal =
_mm256_add_ps(avgPointsVal, _mm256_and_ps(compareMask, dataPointsVal));
// Count the number of bins which do not exceed the mean amplitude
vValidBinCount =
_mm256_add_ps(vValidBinCount, _mm256_and_ps(compareMask, vOnesVector));
}
// Calculate the mean from the remaining data points
_mm256_storeu_ps(avgPointsVector, avgPointsVal);
sumMean = 0.0;
sumMean += avgPointsVector[0];
sumMean += avgPointsVector[1];
sumMean += avgPointsVector[2];
sumMean += avgPointsVector[3];
sumMean += avgPointsVector[4];
sumMean += avgPointsVector[5];
sumMean += avgPointsVector[6];
sumMean += avgPointsVector[7];
// Calculate the number of valid bins from the remaining count
__VOLK_ATTR_ALIGNED(16) float validBinCountVector[8];
_mm256_storeu_ps(validBinCountVector, vValidBinCount);
float validBinCount = 0;
validBinCount += validBinCountVector[0];
validBinCount += validBinCountVector[1];
validBinCount += validBinCountVector[2];
validBinCount += validBinCountVector[3];
validBinCount += validBinCountVector[4];
validBinCount += validBinCountVector[5];
validBinCount += validBinCountVector[6];
validBinCount += validBinCountVector[7];
number = eighthPoints * 8;
for (; number < num_points; number++) {
if (realDataPoints[number] <= meanAmplitude) {
sumMean += realDataPoints[number];
validBinCount += 1.0;
}
}
float localNoiseFloorAmplitude = 0;
if (validBinCount > 0.0) {
localNoiseFloorAmplitude = sumMean / validBinCount;
} else {
localNoiseFloorAmplitude =
meanAmplitude; // For the odd case that all the amplitudes are equal...
}
*noiseFloorAmplitude = localNoiseFloorAmplitude;
}
#endif /* LV_HAVE_AVX */
#ifdef LV_HAVE_RVV
#include <riscv_vector.h>
static inline void
volk_32f_s32f_calc_spectral_noise_floor_32f_rvv(float* noiseFloorAmplitude,
const float* realDataPoints,
const float spectralExclusionValue,
const unsigned int num_points)
{
float sum;
volk_32f_accumulator_s32f_rvv(&sum, realDataPoints, num_points);
float meanAmplitude = sum / num_points + spectralExclusionValue;
vfloat32m8_t vbin = __riscv_vfmv_v_f_f32m8(meanAmplitude, __riscv_vsetvlmax_e32m8());
vfloat32m8_t vsum = __riscv_vfmv_v_f_f32m8(0, __riscv_vsetvlmax_e32m8());
size_t n = num_points, binCount = 0;
for (size_t vl; n > 0; n -= vl, realDataPoints += vl) {
vl = __riscv_vsetvl_e32m8(n);
vfloat32m8_t v = __riscv_vle32_v_f32m8(realDataPoints, vl);
vbool4_t m = __riscv_vmfle(v, vbin, vl);
binCount += __riscv_vcpop(m, vl);
vsum = __riscv_vfadd_tumu(m, vsum, vsum, v, vl);
}
size_t vl = __riscv_vsetvlmax_e32m1();
vfloat32m1_t v = RISCV_SHRINK8(vfadd, f, 32, vsum);
vfloat32m1_t z = __riscv_vfmv_s_f_f32m1(0, vl);
sum = __riscv_vfmv_f(__riscv_vfredusum(v, z, vl));
*noiseFloorAmplitude = binCount == 0 ? meanAmplitude : sum / binCount;
}
#endif /*LV_HAVE_RVV*/
#endif /* INCLUDED_volk_32f_s32f_calc_spectral_noise_floor_32f_u_H */