优化 ：NEON右移变左移

最新推荐文章于 2024-10-22 21:27:43 发布
最新推荐文章于 2024-10-22 21:27:43 发布
阅读量449 收藏
点赞数
CC 4.0 BY-SA版权
分类专栏： arm汇编
版权声明：本文为博主原创文章，遵循 CC 4.0 BY-SA 版权协议，转载请附上原文出处链接和本声明。
本文链接：https://blog.youkuaiyun.com/wuqi1003/article/details/104101449
本文探讨了从ARM汇编语言转换到NEON指令集时的特殊技巧，特别是关于移位操作的处理。文章指出，在进行立即数移位时，左移和右移均可使用，并包含饱和操作；但在变量移位中，仅左移适用，且右移需转换为左移操作。通过具体示例，如将c=a-b,d>>c转换为c=b-a,d<<c，展示了正确的转换方法。

摘要生成于 C知道 ，由 DeepSeek-R1 满血版支持， 前往体验 >

按照立即数移位，左右移都可以，且都有饱和操作。

按照变量移位，只有左移可用。

在ARM汇编转NEON时，按变量右移会切换为左移。

即c = a-b, d＞＞c   要写成   c = b-a, d＜＜c 。

; C语言：a=SE_L_shr(tmp1, SE_sub(Q_tmp,1));

;q0=tmp1   q1=Q_tmp

vmov.s32    q14,#1

vsub.s32     q3,q14,q1       ;原本应是q1-q14

vqshl.s32     q2,q0,q3        ;原本是右移改成左移

【NEON 和 VFP 编程】NEON移位指令
洪伟的专栏
11-13 1127
本节包括以下小节： • VSHL、VQSHL、VQSHLU 和 VSHLL（按立即数） 按立即值左移。 • V{Q}{R}SHL（按有符号变量） 按有符号变量左移。 • V{R}SHR{N}、V{R}SRA（按立即数） 按立即值右移。 • VQ{R}SHR{U}N（按立即数） 按立即值右移并进行饱和。 • VSLI 和 VSRI 左移并插入，右移并插入。 一、VSHL、VQSHL、VQSHLU 和...
【ARMv8 SIMD和浮点指令编程】NEON 移位指令——左右移位之术
洪伟的专栏
07-22 611
NEON 移位指令主要涉及逻辑移位、算术移位两大类，同时下面还介绍了两个移位插入指令。
ARM处理器NEON编程及优化技巧—左移右移等移位操作
ceasar11的专栏
02-19 2322
ARM的NEON协处理器技术是一个64/128-bit的混合SIMD架构，用于加速包括视频编码解码、音频解码编码、3D图像、语音和图像等多媒体和信号处理应用。本文主要介绍如何使用NEON的汇编程序来写SIMD的代码，包括如何开始NEON的开发，如何高效的利用NEON。首先会关注内存操作，即如何变更指令来灵活有效的加载和存储数据。接下来是由于SIMD指令的应用而导致剩下的若干个单元的处理，然后是用一
NEON编码 - 第4部分: 左右移位
蓝松SDK
01-11 2585
转自：http://blogs.arm.com/software-enablement/521-neon%E7%BC%96%E7%A0%81-%E7%AC%AC4%E9%83%A8%E5%88%86-%E5%B7%A6%E5%8F%B3%E7%A7%BB%E4%BD%8D/ NEON编码 - 第4部分: 左右移位 Posted by ARM Martyn,   1 COM
neon指令，注意事项
weixin_30858241的博客
11-01 209
1. vbic_s8(int8x8_t a,int8x8_t b) 是 ~(ai&bi)，一开始理解成 (~ai )&bi 导致出错 2.uint8x8_tvqshrn_n_u16(uint16x8_t__a,constint__b); 饱和窄型右移 uint8x8_tvshrn_n_u16(uint16x8_t__a,constint...
【ARMv8/ARMv9 硬件加速系列 2.2 -- ARM NEON 的加减乘除(左移右移)运算】
CodingCos的博客
06-18 1055
最后，这个示例是基于假设的代码片段，具体实现时根据目标环境和需求可能需要做相应的调整。加载数据，对它们进行加、减和乘,左移和右移操作。最后，我们会将结果存储到内存地址。ARMv8的SIMD指令集允许对向量寄存器中的多个数据进行并行操作。指令使用了后置更新地址的写法，每次存储后都会更新。下面代码是使用ARMv8汇编语言对向量寄存器。执行加、减、乘以及左移和右移操作的示例。寄存器的值，为下一次存储准备。处, 方便观察结果。
ARM SIMD 指令集：NEON 简介
最新发布
生活需要深度
10-22 677
NEON 还提供了数组向量数据类型，命名模式如下：xx_t，eg：int8x16x4_t 是一个长度为 4 的数组，每一个数据的类型为 int8x16_t。w：表示 wide，第一个输入向量和输出向量类型一样，且是第二个输入向量元素长度的 2 倍，uint16x8_t vsubw_u8(uint16x8_t a, uint8x8_t b);// 将 a, b 向量的相邻数据进行两两和操作。
性能优化（CPU优化技术）-NEON指令介绍
发狂的小花的博客
01-22 2608
本文接下来会详细的介绍 Armv7 和 Armv8 架构下 NEON 向量寄存器、NEON 汇编指令格式、NEON Intrinsics 指令格式、常用的 Intrinsics 指令以及作用、在 x86 平台调试 NEON 代码，最后针对几个常用的 Intrinsics 指令结合实例进行说明。相比于汇编指令，NEON Intrinsics 是一种更简单的编写 NEON 代码的方法，NEON Intrinsics 类似于 C 函数调用，在编译时由编译器替换为相应的汇编指令，使用时需要包含头文件。
【ARM程序设计深度】：LSL逻辑左移，数据处理的极致优化案例
[【ARM程序设计深度】：LSL逻辑左移，数据处理的极致优化案例](https://media.cheggcdn.com/media/a18/a186beee-eecf-40b3-9e8d-02fdfe687796/phpvtHEMj) # 摘要 ARM架构作为移动计算领域的重要基石，其指令集优化...
neon指令硬件加速_CodingForNeon.pdf
01-09
NEON支持各种类型的移位操作，包括逻辑移位和算术移位，可以对数据进行快速的位左移、右移，增强计算灵活性。 综上所述，`Coding for Neon`这份文档详细阐述了如何利用NEON指令集在ARM平台上实现硬件加速，涵盖了从...
NEON-intrinsics.pdf
05-18
arm neon simd
ARM指令集
a3121772305的博客
05-16 658
ARM处理器有9种寻址方式： 1、寄存器寻址 操作数的值在寄存器中，指令中的地址码字段指出的是寄存器编号，指令执行时直接取出寄存器值操作。 寄存器寻址指令举例如下： MOV R1,R2 ;R2->R1 SUB R0,R1,R2 ;R1-R2->R0 2、立即寻址 立即寻址指令中的操作码字段后面的地址码部分就是操作数本身，也就是说，数据就包含在指令当中，取出指令也就取出了可以立即使用的操作数(立即数)。 ...
汇编指令（四）移位指令
weirdo_cy的博客
11-12 1万+
学习概要 格式 移位指令主要分四种 一、逻辑移位指令 1.逻辑左移指令SHL 2.逻辑右移指令SHR 3.逻辑移位指令的功能 二、算术移位指令 1.算术左移指令SAL 2.算术右移指令SAR 最高位不变的意思就是，最高位原来是1（0），右移过后最高位就补1（0）。 3.算术移位指令的功能 三、循环移位指令 1.循环左移指令ROL 2.循环右移指令ROR 四、带进位的循环移位指令 1.带进位的循环左移指令RCL 2.带进位的循环右移指令 移位指令对标志位的影响 1
NEON 常用函数及其执行结果
ShaderJoy 的兴趣技术杂货铺
03-25 9780
令初始数据为： float d0[4] = {0.f, 1.f, 2.f, 3.f}; float d1[4] = {4.f, 5.f, 6.f, 7.f}; float d2[4] = {8.f, 9.f, 10.f, 11.f}; float d3[4] = {12.f, 13.f, 14.f, 15.f}; 一、基本的加载存储操作 1. vld1q_f32 float32x4...
ARM和NEON指令
热门推荐
学无止境
10-15 5万+
在移动平台上进行一些复杂算法的开发，一般需要用到指令集来进行加速。目前在移动上使用最多的是ARM芯片。 ARM是微处理器行业的一家知名企业，其芯片结构有：armv5、armv6、armv7和armv8系列。芯片类型有：arm7、arm9、arm11、cortex系列。指令集有：armv5、armv6和neon指令。关于ARM到知识参考：http://baike.baidu.com/view/11
NEON优化——OpenCV WarpAffine最近邻
风语的专栏
11-23 3098
warpAffine一种典型的应用场景是将camera拍到的图像中人脸抠出来，通过变换输出一张正脸，然后再做一些人脸识别，关键点检测之类的运算。所以通常是输入尺寸固定，输出尺寸也固定，变的是转换矩阵。 最近邻的优势是计算量小，速度较快，问题是放大的情况下锯齿较明显，对于通常是缩小的应用场景最近邻是比较合适的，如果希望在所有的场景下有相对更好的效果，可以考虑双线性。 算法要点 warpAffine和...
arm 饱和指令_ARM指令集速查
weixin_39753584的博客
12-22 703
。作为，包含PC。APSR(应用程序状态寄存器)、CPSR(当前处理器状态寄存器)或SPSR(保存的处理器状态寄存器)nzcvq(ALU标记PSR[31:27])或g(SIMDGE标记PSR[19:16])C*，V*在体系结构v4及更早版本中，标记不可预知；在体系结构v5及以后版本中，标记保持不变。§请参阅表ARM体系结构版本。可为Rs或一个立即数移位值。每种移位类型的允许值与+/-+或–。(+...
CUDA __global__ function 参数分析
OpenHero 开勇
02-13 1910
在论坛里面讨论到一个问题，__global__函数里面传递的参数，到底是怎么传输到每一个thread的，然后做了以下的一些分析； 这个是问题讨论帖子：http://topic.youkuaiyun.com/u/20090210/22/2d9ac353-9606-4fa3-9dee-9d41d7fb2b40.html   C/C++ code __global__ static void HelloCUD
arm中的饱和指令
JefferyZou
11-17 6222
转自--- http://www.cnblogs.com/c6000/archive/2010/11/08/1872223.html ARMv6 及更高版本中推出了饱和指令：SSAT 和 USAT， SSAT16 和 USAT16 有符号饱和到任何位位置和无符号饱和到任何位位置，可选择在饱和前进行移位。 SSAT 可将有符号值饱和到有符号范围内。 USAT 可将有符号值
评论
添加红包

请填写红包祝福语或标题

个

红包个数最小为10个

元

红包金额最低5元

当前余额3.43元 前往充值 >
需支付：10.00元
成就一亿技术人!
领取后你会自动成为博主和红包主的粉丝 规则
hope_wisdom
发出的红包
实付元
使用余额支付
点击重新获取
扫码支付
钱包余额 0

抵扣说明：

1.余额是钱包充值的虚拟货币，按照1:1的比例进行支付金额的抵扣。
2.余额无法直接购买下载，可以购买VIP、付费专栏及课程。

余额充值