15821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// Copyright (c) 2012 The Chromium Authors. All rights reserved. 25821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// Use of this source code is governed by a BSD-style license that can be 35821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// found in the LICENSE file. 45821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 5b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// Initial input buffer layout, dividing into regions r0_ to r4_ (note: r0_, r3_ 6b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// and r4_ will move after the first load): 75821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 85821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// |----------------|-----------------------------------------|----------------| 95821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 10b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// request_frames_ 115821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// <---------------------------------------------------------> 12b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r0_ (during first load) 135821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 145821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// kKernelSize / 2 kKernelSize / 2 kKernelSize / 2 kKernelSize / 2 155821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// <---------------> <---------------> <---------------> <---------------> 165821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// r1_ r2_ r3_ r4_ 175821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 18b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// block_size_ == r4_ - r2_ 19b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// <---------------------------------------> 20b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 21b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// request_frames_ 22b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// <------------------ ... -----------------> 23b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r0_ (during second load) 24b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 25b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// On the second request r0_ slides to the right by kKernelSize / 2 and r3_, r4_ 26b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// and block_size_ are reinitialized via step (3) in the algorithm below. 27b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 28b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// These new regions remain constant until a Flush() occurs. While complicated, 29b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// this allows us to reduce jitter by always requesting the same amount from the 30b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// provided callback. 315821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 325821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// The algorithm: 335821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 34b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 1) Allocate input_buffer of size: request_frames_ + kKernelSize; this ensures 35b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// there's enough room to read request_frames_ from the callback into region 36b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r0_ (which will move between the first and subsequent passes). 37b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 38b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 2) Let r1_, r2_ each represent half the kernel centered around r0_: 39b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 40b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r0_ = input_buffer_ + kKernelSize / 2 41b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r1_ = input_buffer_ 42b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r2_ = r0_ 43b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 44b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r0_ is always request_frames_ in size. r1_, r2_ are kKernelSize / 2 in 45b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// size. r1_ must be zero initialized to avoid convolution with garbage (see 46b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// step (5) for why). 47b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 48b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 3) Let r3_, r4_ each represent half the kernel right aligned with the end of 49b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r0_ and choose block_size_ as the distance in frames between r4_ and r2_: 50b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 51b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r3_ = r0_ + request_frames_ - kKernelSize 52b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r4_ = r0_ + request_frames_ - kKernelSize / 2 53b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// block_size_ = r4_ - r2_ = request_frames_ - kKernelSize / 2 54b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 55b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 4) Consume request_frames_ frames into r0_. 56b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 57b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 5) Position kernel centered at start of r2_ and generate output frames until 58b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// the kernel is centered at the start of r4_ or we've finished generating 59b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// all the output frames. 60b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 61b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 6) Wrap left over data from the r3_ to r1_ and r4_ to r2_. 62b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 63b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 7) If we're on the second load, in order to avoid overwriting the frames we 64b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// just wrapped from r4_ we need to slide r0_ to the right by the size of 65b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r4_, which is kKernelSize / 2: 66b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 67b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r0_ = r0_ + kKernelSize / 2 = input_buffer_ + kKernelSize 68b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 69b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// r3_, r4_, and block_size_ then need to be reinitialized, so goto (3). 70b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 71b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)// 8) Else, if we're not on the second load, goto (4). 725821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// 735821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// Note: we're glossing over how the sub-sample handling works with 745821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// |virtual_source_idx_|, etc. 755821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 765821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)// MSVC++ requires this to be set before any other includes to get M_PI. 775821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#define _USE_MATH_DEFINES 785821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 795821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#include "media/base/sinc_resampler.h" 805821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 815821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#include <cmath> 82c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles)#include <limits> 835821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 845821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#include "base/cpu.h" 855821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#include "base/logging.h" 865821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 875821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#if defined(ARCH_CPU_ARM_FAMILY) && defined(USE_NEON) 885821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#include <arm_neon.h> 895821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#endif 905821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 915821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)namespace media { 925821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 93c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles)static double SincScaleFactor(double io_ratio) { 94c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // |sinc_scale_factor| is basically the normalized cutoff frequency of the 95c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // low-pass filter. 96c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) double sinc_scale_factor = io_ratio > 1.0 ? 1.0 / io_ratio : 1.0; 97c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) 98c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // The sinc function is an idealized brick-wall filter, but since we're 99c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // windowing it the transition from pass to stop does not happen right away. 100c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // So we should adjust the low pass filter cutoff slightly downward to avoid 101c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // some aliasing at the very high-end. 102c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // TODO(crogers): this value is empirical and to be more exact should vary 103c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // depending on kKernelSize. 104c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) sinc_scale_factor *= 0.9; 105c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) 106c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) return sinc_scale_factor; 107c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles)} 108c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) 10990dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)// If we know the minimum architecture at compile time, avoid CPU detection. 11090dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)// Force NaCl code to use C routines since (at present) nothing there uses these 11158537e28ecd584eab876aee8be7156509866d23aTorne (Richard Coles)// methods and plumbing the -msse built library is non-trivial. 11258537e28ecd584eab876aee8be7156509866d23aTorne (Richard Coles)#if defined(ARCH_CPU_X86_FAMILY) && !defined(OS_NACL) 11390dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#if defined(__SSE__) 11490dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#define CONVOLVE_FUNC Convolve_SSE 11590dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)void SincResampler::InitializeCPUSpecificFeatures() {} 11690dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#else 11790dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)// X86 CPU detection required. Functions will be set by 11890dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)// InitializeCPUSpecificFeatures(). 11990dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)// TODO(dalecurtis): Once Chrome moves to an SSE baseline this can be removed. 12090dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#define CONVOLVE_FUNC g_convolve_proc_ 12190dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles) 12290dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)typedef float (*ConvolveProc)(const float*, const float*, const float*, double); 12390dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)static ConvolveProc g_convolve_proc_ = NULL; 12490dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles) 12590dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)void SincResampler::InitializeCPUSpecificFeatures() { 12690dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles) CHECK(!g_convolve_proc_); 12790dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles) g_convolve_proc_ = base::CPU().has_sse() ? Convolve_SSE : Convolve_C; 12890dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)} 12990dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#endif 13090dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#elif defined(ARCH_CPU_ARM_FAMILY) && defined(USE_NEON) 13190dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#define CONVOLVE_FUNC Convolve_NEON 13290dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)void SincResampler::InitializeCPUSpecificFeatures() {} 13390dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#else 13490dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)// Unknown architecture. 13590dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#define CONVOLVE_FUNC Convolve_C 13690dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)void SincResampler::InitializeCPUSpecificFeatures() {} 13790dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles)#endif 13890dce4d38c5ff5333bea97d859d4e484e27edf0cTorne (Richard Coles) 139b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)SincResampler::SincResampler(double io_sample_rate_ratio, 1407dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch int request_frames, 141b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) const ReadCB& read_cb) 1425821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) : io_sample_rate_ratio_(io_sample_rate_ratio), 1435821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) read_cb_(read_cb), 144b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) request_frames_(request_frames), 145b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) input_buffer_size_(request_frames_ + kKernelSize), 1465821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Create input buffers with a 16-byte alignment for SSE optimizations. 1475821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) kernel_storage_(static_cast<float*>( 1485821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) base::AlignedAlloc(sizeof(float) * kKernelStorageSize, 16))), 149c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_pre_sinc_storage_(static_cast<float*>( 150c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) base::AlignedAlloc(sizeof(float) * kKernelStorageSize, 16))), 151c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_window_storage_(static_cast<float*>( 152c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) base::AlignedAlloc(sizeof(float) * kKernelStorageSize, 16))), 1535821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) input_buffer_(static_cast<float*>( 154b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) base::AlignedAlloc(sizeof(float) * input_buffer_size_, 16))), 1555821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) r1_(input_buffer_.get()), 1564e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) r2_(input_buffer_.get() + kKernelSize / 2), 1574e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) currently_resampling_(0) { 1587dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch CHECK_GT(request_frames_, 0); 159b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) Flush(); 1607dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch CHECK_GT(block_size_, kKernelSize) 161b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) << "block_size must be greater than kKernelSize!"; 1625821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 1635821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) memset(kernel_storage_.get(), 0, 1645821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) sizeof(*kernel_storage_.get()) * kKernelStorageSize); 165c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) memset(kernel_pre_sinc_storage_.get(), 0, 166c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) sizeof(*kernel_pre_sinc_storage_.get()) * kKernelStorageSize); 167c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) memset(kernel_window_storage_.get(), 0, 168c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) sizeof(*kernel_window_storage_.get()) * kKernelStorageSize); 1695821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 1705821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) InitializeKernel(); 1715821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} 1725821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 1734e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles)SincResampler::~SincResampler() { 1744e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) // TODO(dalecurtis): Remove debugging for http://crbug.com/295278 1754e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) CHECK(base::AtomicRefCountIsZero(¤tly_resampling_)); 1764e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles)} 1775821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 178b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)void SincResampler::UpdateRegions(bool second_load) { 179b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // Setup various region pointers in the buffer (see diagram above). If we're 180b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // on the second load we need to slide r0_ to the right by kKernelSize / 2. 181b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) r0_ = input_buffer_.get() + (second_load ? kKernelSize : kKernelSize / 2); 182b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) r3_ = r0_ + request_frames_ - kKernelSize; 183b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) r4_ = r0_ + request_frames_ - kKernelSize / 2; 184b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) block_size_ = r4_ - r2_; 185b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) 186b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // r1_ at the beginning of the buffer. 187b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) CHECK_EQ(r1_, input_buffer_.get()); 188b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // r1_ left of r2_, r4_ left of r3_ and size correct. 189b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) CHECK_EQ(r2_ - r1_, r4_ - r3_); 190b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // r2_ left of r3. 191b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) CHECK_LT(r2_, r3_); 192b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)} 193b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) 1945821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)void SincResampler::InitializeKernel() { 1955821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Blackman window parameters. 1965821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) static const double kAlpha = 0.16; 1975821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) static const double kA0 = 0.5 * (1.0 - kAlpha); 1985821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) static const double kA1 = 0.5; 1995821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) static const double kA2 = 0.5 * kAlpha; 2005821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 2015821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Generates a set of windowed sinc() kernels. 2025821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // We generate a range of sub-sample offsets from 0.0 to 1.0. 203c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const double sinc_scale_factor = SincScaleFactor(io_sample_rate_ratio_); 2045821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) for (int offset_idx = 0; offset_idx <= kKernelOffsetCount; ++offset_idx) { 205c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const float subsample_offset = 206c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) static_cast<float>(offset_idx) / kKernelOffsetCount; 2075821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 2085821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) for (int i = 0; i < kKernelSize; ++i) { 209c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const int idx = i + offset_idx * kKernelSize; 210c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const float pre_sinc = M_PI * (i - kKernelSize / 2 - subsample_offset); 211c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_pre_sinc_storage_[idx] = pre_sinc; 2125821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 2135821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Compute Blackman window, matching the offset of the sinc(). 214c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const float x = (i - subsample_offset) / kKernelSize; 215c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const float window = kA0 - kA1 * cos(2.0 * M_PI * x) + kA2 2165821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) * cos(4.0 * M_PI * x); 217c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_window_storage_[idx] = window; 218c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) 219c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // Compute the sinc with offset, then window the sinc() function and store 220c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // at the correct offset. 221c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) if (pre_sinc == 0) { 222c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_storage_[idx] = sinc_scale_factor * window; 223c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) } else { 224c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_storage_[idx] = 225c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) window * sin(sinc_scale_factor * pre_sinc) / pre_sinc; 226c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) } 227c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) } 228c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) } 229c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles)} 230c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) 231c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles)void SincResampler::SetRatio(double io_sample_rate_ratio) { 232c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) if (fabs(io_sample_rate_ratio_ - io_sample_rate_ratio) < 233c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) std::numeric_limits<double>::epsilon()) { 234c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) return; 235c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) } 236c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) 237c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) io_sample_rate_ratio_ = io_sample_rate_ratio; 2385821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 239c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // Optimize reinitialization by reusing values which are independent of 240c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) // |sinc_scale_factor|. Provides a 3x speedup. 241c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const double sinc_scale_factor = SincScaleFactor(io_sample_rate_ratio_); 242c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) for (int offset_idx = 0; offset_idx <= kKernelOffsetCount; ++offset_idx) { 243c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) for (int i = 0; i < kKernelSize; ++i) { 244c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const int idx = i + offset_idx * kKernelSize; 245c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const float window = kernel_window_storage_[idx]; 246c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) const float pre_sinc = kernel_pre_sinc_storage_[idx]; 247c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) 248c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) if (pre_sinc == 0) { 249c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_storage_[idx] = sinc_scale_factor * window; 250c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) } else { 251c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) kernel_storage_[idx] = 252c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) window * sin(sinc_scale_factor * pre_sinc) / pre_sinc; 253c2e0dbddbe15c98d52c4786dac06cb8952a8ae6dTorne (Richard Coles) } 2545821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) } 2555821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) } 2565821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} 2575821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 258b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles)void SincResampler::Resample(int frames, float* destination) { 2594e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) base::AtomicRefCountInc(¤tly_resampling_); 2604e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) 2615821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) int remaining_frames = frames; 2625821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 2635821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Step (1) -- Prime the input buffer at the start of the input stream. 2647dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch if (!buffer_primed_ && remaining_frames) { 265b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) read_cb_.Run(request_frames_, r0_); 2665821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) buffer_primed_ = true; 2675821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) } 2685821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 2697dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch // Step (2) -- Resample! const what we can outside of the loop for speed. It 2707dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch // actually has an impact on ARM performance. See inner loop comment below. 2717dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch const double current_io_ratio = io_sample_rate_ratio_; 2727dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch const float* const kernel_ptr = kernel_storage_.get(); 2735821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) while (remaining_frames) { 2747dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch // |i| may be negative if the last Resample() call ended on an iteration 2757dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch // that put |virtual_source_idx_| over the limit. 2767dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch // 2777dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch // Note: The loop construct here can severely impact performance on ARM 2787dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch // or when built with clang. See https://codereview.chromium.org/18566009/ 2797dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch for (int i = ceil((block_size_ - virtual_source_idx_) / current_io_ratio); 2807dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch i > 0; --i) { 2817dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch DCHECK_LT(virtual_source_idx_, block_size_); 2827dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch 2835821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // |virtual_source_idx_| lies in between two kernel offsets so figure out 2845821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // what they are. 285b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) const int source_idx = virtual_source_idx_; 286b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) const double subsample_remainder = virtual_source_idx_ - source_idx; 2875821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 288b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) const double virtual_offset_idx = 289b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) subsample_remainder * kKernelOffsetCount; 290b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) const int offset_idx = virtual_offset_idx; 2915821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 2925821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // We'll compute "convolutions" for the two kernels which straddle 2935821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // |virtual_source_idx_|. 2947dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch const float* const k1 = kernel_ptr + offset_idx * kKernelSize; 2957dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch const float* const k2 = k1 + kKernelSize; 2965821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 2972a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles) // Ensure |k1|, |k2| are 16-byte aligned for SIMD usage. Should always be 2982a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles) // true so long as kKernelSize is a multiple of 16. 2992a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles) DCHECK_EQ(0u, reinterpret_cast<uintptr_t>(k1) & 0x0F); 3002a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles) DCHECK_EQ(0u, reinterpret_cast<uintptr_t>(k2) & 0x0F); 3012a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles) 3025821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Initialize input pointer based on quantized |virtual_source_idx_|. 3037dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch const float* const input_ptr = r1_ + source_idx; 3045821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3055821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Figure out how much to weight each kernel's "convolution". 306b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) const double kernel_interpolation_factor = 307b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) virtual_offset_idx - offset_idx; 3082a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles) *destination++ = CONVOLVE_FUNC( 3095821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) input_ptr, k1, k2, kernel_interpolation_factor); 3105821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3115821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Advance the virtual index. 3127dbb3d5cf0c15f500944d211057644d6a2f37371Ben Murdoch virtual_source_idx_ += current_io_ratio; 3135821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3144e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) if (!--remaining_frames) { 3154e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) CHECK(!base::AtomicRefCountDec(¤tly_resampling_)); 3165821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) return; 3174e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) } 3185821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) } 3195821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3205821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Wrap back around to the start. 321b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) virtual_source_idx_ -= block_size_; 3225821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 323b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // Step (3) -- Copy r3_, r4_ to r1_, r2_. 3245821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // This wraps the last input frames back to the start of the buffer. 325b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) memcpy(r1_, r3_, sizeof(*input_buffer_.get()) * kKernelSize); 326b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) 327b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // Step (4) -- Reinitialize regions if necessary. 328b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) if (r0_ == r2_) 329b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) UpdateRegions(true); 3305821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 331b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) // Step (5) -- Refresh the buffer with more input. 332b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) read_cb_.Run(request_frames_, r0_); 3335821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) } 3344e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) 3354e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) CHECK(!base::AtomicRefCountDec(¤tly_resampling_)); 3365821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} 3375821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3382a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles)#undef CONVOLVE_FUNC 3392a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles) 3402a99a7e74a7f215066514fe81d2bfa6639d9edddTorne (Richard Coles)int SincResampler::ChunkSize() const { 341b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) return block_size_ / io_sample_rate_ratio_; 3425821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} 3435821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3445821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)void SincResampler::Flush() { 3454e180b6a0b4720a9b8e9e959a882386f690f08ffTorne (Richard Coles) CHECK(base::AtomicRefCountIsZero(¤tly_resampling_)); 3465821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) virtual_source_idx_ = 0; 3475821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) buffer_primed_ = false; 348b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) memset(input_buffer_.get(), 0, 349b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) sizeof(*input_buffer_.get()) * input_buffer_size_); 350b2df76ea8fec9e32f6f3718986dba0d95315b29cTorne (Richard Coles) UpdateRegions(false); 3515821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} 3525821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3535821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)float SincResampler::Convolve_C(const float* input_ptr, const float* k1, 3545821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) const float* k2, 3555821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) double kernel_interpolation_factor) { 3565821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) float sum1 = 0; 3575821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) float sum2 = 0; 3585821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3595821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Generate a single output sample. Unrolling this loop hurt performance in 3605821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // local testing. 3615821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) int n = kKernelSize; 3625821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) while (n--) { 3635821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) sum1 += *input_ptr * *k1++; 3645821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) sum2 += *input_ptr++ * *k2++; 3655821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) } 3665821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3675821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Linearly interpolate the two "convolutions". 3685821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) return (1.0 - kernel_interpolation_factor) * sum1 3695821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) + kernel_interpolation_factor * sum2; 3705821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} 3715821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3725821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#if defined(ARCH_CPU_ARM_FAMILY) && defined(USE_NEON) 3735821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)float SincResampler::Convolve_NEON(const float* input_ptr, const float* k1, 3745821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) const float* k2, 3755821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) double kernel_interpolation_factor) { 3765821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) float32x4_t m_input; 3775821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) float32x4_t m_sums1 = vmovq_n_f32(0); 3785821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) float32x4_t m_sums2 = vmovq_n_f32(0); 3795821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3805821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) const float* upper = input_ptr + kKernelSize; 3815821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) for (; input_ptr < upper; ) { 3825821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) m_input = vld1q_f32(input_ptr); 3835821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) input_ptr += 4; 3845821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) m_sums1 = vmlaq_f32(m_sums1, m_input, vld1q_f32(k1)); 3855821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) k1 += 4; 3865821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) m_sums2 = vmlaq_f32(m_sums2, m_input, vld1q_f32(k2)); 3875821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) k2 += 4; 3885821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) } 3895821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3905821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Linearly interpolate the two "convolutions". 3915821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) m_sums1 = vmlaq_f32( 3925821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) vmulq_f32(m_sums1, vmovq_n_f32(1.0 - kernel_interpolation_factor)), 3935821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) m_sums2, vmovq_n_f32(kernel_interpolation_factor)); 3945821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 3955821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) // Sum components together. 3965821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) float32x2_t m_half = vadd_f32(vget_high_f32(m_sums1), vget_low_f32(m_sums1)); 3975821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) return vget_lane_f32(vpadd_f32(m_half, m_half), 0); 3985821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} 3995821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)#endif 4005821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles) 4015821806d5e7f356e8fa4b058a389a808ea183019Torne (Richard Coles)} // namespace media 402