ZYNQ的双核A9移植ARM DSP库也是没问题的，很多函数也做了NEON指令加速，使能宏定义ARM_MATH_NEON即可，爽歪歪

eric2013

专门为A核信号处理而做，爽爽爽！

以下面函数为例：

1. /* ----------------------------------------------------------------------
   
2. * Project:      CMSIS DSP Library
   
3. * Title:        arm_braycurtis_distance_f32.c
   
4. * Description:  Bray-Curtis distance between two vectors
   
5. *
   
6. * $Date:        23 April 2021
   
7. * $Revision:    V1.9.0
   
8. *
   
9. * Target Processor: Cortex-M and Cortex-A cores
   
10. * -------------------------------------------------------------------- */
    
11. /*
    
12. * Copyright (C) 2010-2021 ARM Limited or its affiliates. All rights reserved.
    
13. *
    
14. * SPDX-License-Identifier: Apache-2.0
    
15. *
    
16. * Licensed under the Apache License, Version 2.0 (the License); you may
    
17. * not use this file except in compliance with the License.
    
18. * You may obtain a copy of the License at
    
19. *
    
20. * www.apache.org/licenses/LICENSE-2.0
    
21. *
    
22. * Unless required by applicable law or agreed to in writing, software
    
23. * distributed under the License is distributed on an AS IS BASIS, WITHOUT
    
24. * WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
    
25. * See the License for the specific language governing permissions and
    
26. * limitations under the License.
    
27. */
    
28. 
    
29. #include "dsp/distance_functions.h"
    
30. #include <limits.h>
    
31. #include <math.h>
    
32. 
    
33. 
    
34. 
    
35. /**
    
36.   @addtogroup braycurtis
    
37.   @{
    
38. */
    
39. 
    
40. 
    
41. /**
    
42. * @brief        Bray-Curtis distance between two vectors
    
43. * @param[in]    pA         First vector
    
44. * @param[in]    pB         Second vector
    
45. * @param[in]    blockSize  vector length
    
46. * @return distance
    
47. *
    
48. */
    
49. #if defined(ARM_MATH_MVEF) && !defined(ARM_MATH_AUTOVECTORIZE)
    
50. 
    
51. #include "arm_helium_utils.h"
    
52. 
    
53. float32_t arm_braycurtis_distance_f32(const float32_t *pA,const float32_t *pB, uint32_t blockSize)
    
54. {
    
55.     float32_t       accumDiff = 0.0f, accumSum = 0.0f;
    
56.     uint32_t        blkCnt;
    
57.     f32x4_t         a, b, c, accumDiffV, accumSumV;
    
58. 
    
59. 
    
60.     accumDiffV = vdupq_n_f32(0.0f);
    
61.     accumSumV = vdupq_n_f32(0.0f);
    
62. 
    
63.     blkCnt = blockSize >> 2;
    
64.     while (blkCnt > 0) {
    
65.         a = vld1q(pA);
    
66.         b = vld1q(pB);
    
67. 
    
68.         c = vabdq(a, b);
    
69.         accumDiffV = vaddq(accumDiffV, c);
    
70. 
    
71.         c = vaddq_f32(a, b);
    
72.         c = vabsq_f32(c);
    
73.         accumSumV = vaddq(accumSumV, c);
    
74. 
    
75.         pA += 4;
    
76.         pB += 4;
    
77.         blkCnt--;
    
78.     }
    
79. 
    
80.     blkCnt = blockSize & 3;
    
81.     if (blkCnt > 0U) {
    
82.         mve_pred16_t    p0 = vctp32q(blkCnt);
    
83. 
    
84.         a = vldrwq_z_f32(pA, p0);
    
85.         b = vldrwq_z_f32(pB, p0);
    
86. 
    
87.         c = vabdq(a, b);
    
88.         accumDiffV = vaddq_m(accumDiffV, accumDiffV, c, p0);
    
89. 
    
90.         c = vaddq_f32(a, b);
    
91.         c = vabsq_f32(c);
    
92.         accumSumV = vaddq_m(accumSumV, accumSumV, c, p0);
    
93.     }
    
94. 
    
95.     accumDiff = vecAddAcrossF32Mve(accumDiffV);
    
96.     accumSum = vecAddAcrossF32Mve(accumSumV);
    
97. 
    
98.     /*
    
99.        It is assumed that accumSum is not zero. Since it is the sum of several absolute
    
100.        values it would imply that all of them are zero. It is very unlikely for long vectors.
     
101.      */
     
102.     return (accumDiff / accumSum);
     
103. }
     
104. #else
     
105. #if defined(ARM_MATH_NEON)
     
106. 
     
107. #include "NEMath.h"
     
108. 
     
109. float32_t arm_braycurtis_distance_f32(const float32_t *pA,const float32_t *pB, uint32_t blockSize)
     
110. {
     
111.    float32_t accumDiff=0.0f, accumSum=0.0f;
     
112.    uint32_t blkCnt;
     
113.    float32x4_t a,b,c,accumDiffV, accumSumV;
     
114.    float32x2_t accumV2;
     
115. 
     
116.    accumDiffV = vdupq_n_f32(0.0f);
     
117.    accumSumV = vdupq_n_f32(0.0f);
     
118. 
     
119.    blkCnt = blockSize >> 2;
     
120.    while(blkCnt > 0)
     
121.    {
     
122.         a = vld1q_f32(pA);
     
123.         b = vld1q_f32(pB);
     
124. 
     
125.         c = vabdq_f32(a,b);
     
126.         accumDiffV = vaddq_f32(accumDiffV,c);
     
127. 
     
128.         c = vaddq_f32(a,b);
     
129.         c = vabsq_f32(c);
     
130.         accumSumV = vaddq_f32(accumSumV,c);
     
131. 
     
132.         pA += 4;
     
133.         pB += 4;
     
134.         blkCnt --;
     
135.    }
     
136.    accumV2 = vpadd_f32(vget_low_f32(accumDiffV),vget_high_f32(accumDiffV));
     
137.    accumDiff = vget_lane_f32(accumV2, 0) + vget_lane_f32(accumV2, 1);
     
138. 
     
139.    accumV2 = vpadd_f32(vget_low_f32(accumSumV),vget_high_f32(accumSumV));
     
140.    accumSum = vget_lane_f32(accumV2, 0) + vget_lane_f32(accumV2, 1);
     
141. 
     
142.    blkCnt = blockSize & 3;
     
143.    while(blkCnt > 0)
     
144.    {
     
145.       accumDiff += fabsf(*pA - *pB);
     
146.       accumSum += fabsf(*pA++ + *pB++);
     
147.       blkCnt --;
     
148.    }
     
149.    /*
     
150.    It is assumed that accumSum is not zero. Since it is the sum of several absolute
     
151.    values it would imply that all of them are zero. It is very unlikely for long vectors.
     
152.    */
     
153.    return(accumDiff / accumSum);
     
154. }
     
155. 
     
156. #else
     
157. float32_t arm_braycurtis_distance_f32(const float32_t *pA,const float32_t *pB, uint32_t blockSize)
     
158. {
     
159.    float32_t accumDiff=0.0f, accumSum=0.0f, tmpA, tmpB;
     
160. 
     
161.    while(blockSize > 0)
     
162.    {
     
163.       tmpA = *pA++;
     
164.       tmpB = *pB++;
     
165.       accumDiff += fabsf(tmpA - tmpB);
     
166.       accumSum += fabsf(tmpA + tmpB);
     
167.       blockSize --;
     
168.    }
     
169.    /*
     
170.    It is assumed that accumSum is not zero. Since it is the sum of several absolute
     
171.    values it would imply that all of them are zero. It is very unlikely for long vectors.
     
172.    */
     
173.    return(accumDiff / accumSum);
     
174. }
     
175. #endif
     
176. #endif /* defined(ARM_MATH_MVEF) && !defined(ARM_MATH_AUTOVECTORIZE) */
     
177. 
     
178. 
     
179. /**
     
180. * @} end of braycurtis group
     
181. */
     

复制代码

missfox

移植成功了分享下，我好白嫖

eric2013

missfox 发表于 2021-11-19 09:43
移植成功了分享下，我好白嫖

这个可以有。

小黄蜂

看来以后又可以白嫖zynq了，我靠白嫖都快成为公司ARM专家了

luguan1997

它这里面的 fft 算法是支持 neon 的吗，我粗略看了下似乎只有是 mve 的。
是否能移植研究下 Ne10 这个库。 比较下性能。我最近也想研究下算法优化

eric2013

luguan1997 发表于 2021-11-20 14:30
它这里面的 fft 算法是支持 neon 的吗，我粗略看了下似乎只有是 mve 的。
是否能移植研究下 Ne10 这个库。 ...

FFT没有SIMD加速，带硬件FPU就好使。

TerayTech

硬汉哥，请问下可以出个简单的教学教下咱们怎么移植CMSIS-DSP库到ZYNQ么，很想给这个库和NEON用上，然而搜遍全网没啥资料，就这里有一点

venus5712

请问这个DSP库搞咋样啦？？

venus5712

请问这个DSP库搞咋样啦？(不好意思多发了一个，DSP库我下载了一个，地址：Release CMSIS 5.9.0 · ARM-software/CMSIS_5 · GitHub)

战弘宇

请问ZYNQ 移植DSP库有工程吗，可以发出来吗

kl_upc

楼主有没有教程资料啊

kl_upc

这个有教程可以看看吗

cj0220

请问有移植教程了吗？分享一下啊

cj0220

kl_upc 发表于 2023-5-22 13:34
这个有教程可以看看吗

请问你移植成功了吗？分享一下哈

OKeey

可以移植吗，是否需要上系统，裸机能玩吗