GNU Radio Manual and C++ API Reference  3.7.5.1
The Free & Open Software Radio Ecosystem
 All Classes Namespaces Files Functions Variables Typedefs Enumerations Enumerator Properties Friends Macros Groups Pages
volk_32f_x2_max_32f.h
Go to the documentation of this file.
1 #ifndef INCLUDED_volk_32f_x2_max_32f_a_H
2 #define INCLUDED_volk_32f_x2_max_32f_a_H
3 
4 #include <inttypes.h>
5 #include <stdio.h>
6 
7 #ifdef LV_HAVE_SSE
8 #include <xmmintrin.h>
9 /*!
10  \brief Selects maximum value from each entry between bVector and aVector and store their results in the cVector
11  \param cVector The vector where the results will be stored
12  \param aVector The vector to be checked
13  \param bVector The vector to be checked
14  \param num_points The number of values in aVector and bVector to be checked and stored into cVector
15 */
16 static inline void volk_32f_x2_max_32f_a_sse(float* cVector, const float* aVector, const float* bVector, unsigned int num_points){
17  unsigned int number = 0;
18  const unsigned int quarterPoints = num_points / 4;
19 
20  float* cPtr = cVector;
21  const float* aPtr = aVector;
22  const float* bPtr= bVector;
23 
24  __m128 aVal, bVal, cVal;
25  for(;number < quarterPoints; number++){
26 
27  aVal = _mm_load_ps(aPtr);
28  bVal = _mm_load_ps(bPtr);
29 
30  cVal = _mm_max_ps(aVal, bVal);
31 
32  _mm_store_ps(cPtr,cVal); // Store the results back into the C container
33 
34  aPtr += 4;
35  bPtr += 4;
36  cPtr += 4;
37  }
38 
39  number = quarterPoints * 4;
40  for(;number < num_points; number++){
41  const float a = *aPtr++;
42  const float b = *bPtr++;
43  *cPtr++ = ( a > b ? a : b);
44  }
45 }
46 #endif /* LV_HAVE_SSE */
47 
48 #ifdef LV_HAVE_NEON
49 #include <arm_neon.h>
50 /*!
51  \brief Selects maximum value from each entry between bVector and aVector and store their results in the cVector
52  \param cVector The vector where the results will be stored
53  \param aVector The vector to be checked
54  \param bVector The vector to be checked
55  \param num_points The number of values in aVector and bVector to be checked and stored into cVector
56 */
57 static inline void volk_32f_x2_max_32f_neon(float* cVector, const float* aVector, const float* bVector, unsigned int num_points){
58  unsigned int quarter_points = num_points / 4;
59  float* cPtr = cVector;
60  const float* aPtr = aVector;
61  const float* bPtr= bVector;
62  unsigned int number = 0;
63 
64  float32x4_t a_vec, b_vec, c_vec;
65  for(number = 0; number < quarter_points; number++){
66  a_vec = vld1q_f32(aPtr);
67  b_vec = vld1q_f32(bPtr);
68  c_vec = vmaxq_f32(a_vec, b_vec);
69  vst1q_f32(cPtr, c_vec);
70  aPtr += 4;
71  bPtr += 4;
72  cPtr += 4;
73  }
74 
75  for(number = quarter_points*4; number < num_points; number++){
76  const float a = *aPtr++;
77  const float b = *bPtr++;
78  *cPtr++ = ( a > b ? a : b);
79  }
80 
81 }
82 #endif /* LV_HAVE_NEON */
83 
84 #ifdef LV_HAVE_GENERIC
85 /*!
86  \brief Selects maximum value from each entry between bVector and aVector and store their results in the cVector
87  \param cVector The vector where the results will be stored
88  \param aVector The vector to be checked
89  \param bVector The vector to be checked
90  \param num_points The number of values in aVector and bVector to be checked and stored into cVector
91 */
92 static inline void volk_32f_x2_max_32f_generic(float* cVector, const float* aVector, const float* bVector, unsigned int num_points){
93  float* cPtr = cVector;
94  const float* aPtr = aVector;
95  const float* bPtr= bVector;
96  unsigned int number = 0;
97 
98  for(number = 0; number < num_points; number++){
99  const float a = *aPtr++;
100  const float b = *bPtr++;
101  *cPtr++ = ( a > b ? a : b);
102  }
103 }
104 #endif /* LV_HAVE_GENERIC */
105 
106 #ifdef LV_HAVE_ORC
107 /*!
108  \brief Selects maximum value from each entry between bVector and aVector and store their results in the cVector
109  \param cVector The vector where the results will be stored
110  \param aVector The vector to be checked
111  \param bVector The vector to be checked
112  \param num_points The number of values in aVector and bVector to be checked and stored into cVector
113 */
114 extern void volk_32f_x2_max_32f_a_orc_impl(float* cVector, const float* aVector, const float* bVector, unsigned int num_points);
115 static inline void volk_32f_x2_max_32f_u_orc(float* cVector, const float* aVector, const float* bVector, unsigned int num_points){
116  volk_32f_x2_max_32f_a_orc_impl(cVector, aVector, bVector, num_points);
117 }
118 #endif /* LV_HAVE_ORC */
119 
120 
121 #endif /* INCLUDED_volk_32f_x2_max_32f_a_H */