内联汇编必须声明输入/输出约束、clobber列表并加volatile，否则-O2以上优化会导致寄存器冲突、指令被删或结果错误；AT&T语法需%寄存器、$立即数、源→目的顺序，跨平台应优先用intrinsics而非手写asm。
别直接写 asm 字符串——90% 的新手错误都出在没声明输入输出、寄存器冲突或忘了 volatile，导致编译器优化掉关键指令，或者结果根本不对。
gcc/clang 内联汇编必须带四要素：模板、输出、输入、破坏列表
GCC/Clang 的扩展语法不是简单拼字符串，而是结构化声明。漏掉任一要素都可能引发未定义行为：
-
__asm__ __volatile__是标配，volatile阻止编译器删掉或重排指令（比如延时循环、IO 寄存器写入） - 输出部分用
"=r"(var)形式，=表示写入，r表示通用寄存器（编译器自动选） - 输入部分用
"r"(val)或"i"(42)（立即数）、"m"(arr[0])（内存地址） - 破坏列表（clobber list）必须列出所有被修改但未声明为输出的寄存器，比如用了
%ecx却没在输出里绑定，就得写"%ecx"
错误示例：asm("addl %1, %0" : "=r"(result) : "r"(a), "r"(b)); —— 这里 %1 和 %0 指代顺序依赖约束顺序，但没告诉编译器 b 是只读输入，实际可能被误当成输出；正确写法应显式命名或确保约束与占位符严格对应。
AT&T 语法细节：寄存器要加 %，立即数要加 $，操作数顺序是源→目的
GCC 默认用 AT&T 语法，和 Intel 语法（MSVC 用）完全相反，混用必错：
- 寄存器名必须带
%前缀：%eax，不是eax；在约束中引用操作数时用%0、%1，但寄存器本身仍需%%eax（双% 转义） - 立即数必须加
$：movl $42, %eax，写成movl 42, %eax就变成访存地址 42 - 操作数顺序是「源, 目的」：
addl %esi, %edi表示%edi += %esi，不是反过来 - 指令后缀（
b/w/l）建议显式写上，避免编译器猜错字长，尤其涉及al/ax/eax混用时
别用内联汇编替代 intrinsics：SIMD 场景优先选 _mm256_add_ps
想做向量化计算？先查头文件
-
_mm256_add_ps(a, b)是跨平台、类型安全、编译器可优化的封装，比asm("vaddps %1, %2, %0" ::: "xmm0")更可靠 - intrinsics 自动处理寄存器分配、对齐检查、指令选择（AVX vs SSE），而手写 asm 容易因忘记
vzeroupper导致后续 SSE 指令变慢 - 只有当 intrinsics 无法表达语义时才考虑 asm：比如需要精确控制某条指令的编码位置、插入
lfence内存屏障、或调用cpuid获取 CPU 特性
典型陷阱：用 asm 实现原子加法，却忽略 lock 前缀或 x86-64 下 rax 与 eax 的零扩展行为，结果在不同优化等级下表现不一致。
跨平台移植前先问：这代码真需要跑在 ARM 或 RISC-V 上吗？
内联汇编是平台锁死的——x86 的 %rax 在 ARM 上不存在，AT&T 语法在 MSVC 下直接报错：
- 如果目标平台固定（如嵌入式 x86_64 固件），可放心用 GCC 扩展，但必须限定编译器版本（GCC ≥ 10）并加
#ifdef __x86_64__守卫 - 若需多架构支持，要么用条件编译分别实现（ARM 用
__asm__(".arch_extension crc")），要么退回到 C++20std::atomic或编译器 builtin（如__atomic_fetch_add） - 最常被忽略的一点：即使同是 x86_64，Linux System V ABI 和 Windows x64 ABI 对 callee-saved 寄存器定义不同，破坏列表写错会导致函数返回后寄存器值被意外覆盖
真正难的从来不是写出能编译的 asm，而是写出在 -O0 到 -O3、不同 target-cpu、不同链接方式下行为一致的 asm——它要求你同时懂 C++ ABI、汇编语义、编译器中间表示，以及调试时怎么看 objdump -d 输出里哪一行对应你的 asm 块。
C++免费学习笔记（深入）：立即使用
在学习笔记中，你将探索 C++ 的入门与实战技巧！
