摘要：作者：zyl910。一、更新说明1.1 支持VC2012 VC2012增加了很多Intrinsics函数，详见——http://www.cnblogs.com/zyl910/archive/2012/11/06/intrin_vc2012.html检查了一下VC2012新增的Intrinsics函数集，发现它支持ARM指令和Haswell新指令 根据上述信息改进zintrin，检测到是VC2012时定义相关的宏—— #if _MSC_VER >=1700 // VC2012 #define INTRIN_AVX2 1 // immint... 阅读全文

摘要：作者：zyl910 之前我整理了一份VC6至VC2010中Intrinsics函数集对应表。现在VS2012发布了，它有没有增加Intrinsics函数集呢？于是我对此进行检查。 若是64位win8系统中默认安装的VS2012，Intrinsics头文件位于“C:\Program Files (x86)\Microsoft Visual Studio 11.0\VC\include”目录。 首先发现多了两个Intrinsics头文件——armintr.h：ARM的常用指令集。arm_neon.h：ARM的neon指令集。 看了一下intrin.h，发现以前大段的ARM Intrinsi... 阅读全文

摘要：一、popcnt指令简介 popcnt是“population count”的缩写，该操作一般翻译为“位1计数”，即统计有多少个“为1的位”。例如，十六进制数“FF”，它有8个为1的位，即“popcnt(0xFF) = 8”。popcnt主要应用在密码学与通信安全，例如计算汉明重量（Hamming weight）。 x86体系最初是没有硬件popcnt指令的，只能靠软件计算。 2008年底，Intel发布了Nehalem架构的处理器，增加了SSE4.2指令集，其中就有硬件popcnt指令。虽然它名义上是属于SSE4.2指令集，但它并不使用XMM寄存器（SSE的128位寄存器），而是使用G... 阅读全文

摘要：作者：zyl910。 之前的ccpuid V1.00版（http://www.cnblogs.com/zyl910/archive/2012/07/11/ccpuid.html）只支持VC。 现在的V1.01版支持GCC，不仅兼容32位/64位Linux下的GCC，还兼容Windows下的MinGW、MinGW-w64、TDM-GCC等。可以自由的编译为Windows下、或Linux下的程序。一、更新说明 主要的改进有——1. 支持GCC。2. 使用getcpuid/getcpuidex函数来获取CPUID信息。3. 使用C99标准整数类型uint32_t，提高可移植性。二、全部代码2.... 阅读全文

摘要：作者：zyl910 前面我们尝试过在VC中获取CPUID信息。现在再来试试GCC编译器。一、调用CPUID指令 怎么调用CPUID指令呢？有三种办法——1. 用汇编语言编写一个cpuid函数，然后调整链接器配置，在C语言中调用该函数。2. 使用内嵌汇编调用CPUID指令。3. 使用编译器提供的Intrinsics函数来调用CPUID等特定平台指令。 我们一般优先使用第3种办法，代码量少、可读性高、编译维护简单。例如VC（VC2005或更高）在“intrin.h”中声明了 __cpuid函数。 当编译器没有提供Intrinsics函数时，就只有使用前两种办法了。1.1 查找函数 首先，... 阅读全文

摘要：作者：zyl910更多详情见——http://www.cnblogs.com/zyl910/archive/2012/04/26/md00.htmlSIMD函数整理：00 索引贴R：寄存器。M：64位MM寄存器；X：128位XMM寄存器；Y：256位YMM寄存器。Name：函数名。Name2：另一种函数名。功能：功能描述。Asm：汇编指令。PCode：伪代码。RNameName2功能AsmPCodeX_MM_SHUFFLE混洗的掩码.4#http://msdn.microsoft.com/en-us/library/4d3eabky(vs.71).aspxX_MM_TRANSPOSE4_PS矩 阅读全文

摘要：作者：zyl910更多详情见——http://www.cnblogs.com/zyl910/archive/2012/04/26/md00.htmlSIMD函数整理：00 索引贴Name：函数名。Name2：另一种函数名。功能：功能描述。Asm：汇编指令。PCode：伪代码。 NameName2功能AsmPCode_m_empty_mm_emptyMMX状态置空EMMS_m_from_int_mm_cvtsi32_si64加载32位MOVDr=ZX(i)_m_to_int_mm_cvtsi64_si32返回低32位MOVDr=(uD)m_m_packsswb_mm_packs_pi16... 阅读全文

摘要：作者：zyl910 关于获取各种CPUID信息，我之前积累了不少代码，现在决定将它们封装在一个模块中，方便代码复用。 其次，前面只是介绍了CPUID的一些常用功能，而Intel、AMD的手册中定义了大量的CPUID功能。所以我希望有一个程序能按照功能号顺序，依次显示所有的CPUID信息。这样就能很方便的与Intel、AMD的手册进行对照，有助于学习与理解。一、模块设计 最初方案是 想将所有功能全部放在一个“ccpuid.h”头文件中，这样用起来会比较方便。 但是考虑到全局变量等问题，以及需要编写CCPUID类。所以最终决定按照常规做法，分解为头文件与实现文件。 对于原先所写的宏定义、... 阅读全文

摘要：从2011年的Sandy Bridge微架构处理器开始，现在支持AVX系列指令集的处理器越来越多了。本文探讨如何用VC编写检测AVX系列指令集的程序，并利用了先前的CPUIDFIELD方案。一、AVX系列指令集简介 SSE5 指令：SSE5 是一个纸面上的指令集，并没有最终实现，AMD 在 2007 年 8 月公布 SSE5 指令集规范，在 2009 年 5 月 AMD 推出了 XOP，FMA4 以及 CVT16 来取代 SSE5 指令。 AVX 指令：2008 年 3 月 Intel 发布了 AVX（Advanced Vector Extensions）指令集规范，首次在 Sandy B.. 阅读全文

摘要：除了基本的MMX和SSE系列指令集外，x86体系还有其他扩展指令集，例如SSE4A、AES、PCLMULQDQ等，它们也可以利用CPUID指令来检测。但是，这些指令集细碎杂多。如果像以前那样分别编写检测函数的话，那工作量太大，不值得。而且大量的函数名也会给使用带来麻烦。于是文篇探讨如何设计一套通用的检测方案。零、指令简介 SSE4A指令：是AMD提出的，最早出现在2007年的K10微架构的处理器上。它针对Intel的SSE4指令集修改而来，去除其中对I64优化的指令，保留图形、影音编码、3D运算、游戏等多媒体指令，并完全兼容。 AES指令：是Intel提出的，最早出现在2010年的West.. 阅读全文

摘要：以前我写了一篇《[VC6] 检查MMX和SSE系列指令集的支持级别（最高SSE4.2）》（http://www.cnblogs.com/zyl910/archive/2012/03/01/checksimd.html）。现在发现该方法存在两点缺陷——1.不支持64位，因为VC的64位程序不支持内嵌汇编；2.没有区分硬件支持与操作系统支持。 怎么解决这两点缺陷呢？ 对于第1点，可以利用Intrinsics函数来兼容32位和64位。为了更方便的使用CPUID指令，可以利用《如何在各个版本的VC及64位下使用CPUID指令》（http://www.cnblogs.com/zyl910/arc... 阅读全文

摘要：前面我们探讨了在16位的DOS实模式下使用CPUID指令（http://www.cnblogs.com/zyl910/archive/2012/05/14/dos16_getcpuid.html）。而现在64位Windows系统已经很流行了，在32/64位模式下如何使用CPUID呢？于是本文介绍了如何在各个版本的VC及64位下使用CPUID指令。一、推荐使用__cpuid、__cpuidex等Intrinsics函数 在32位模式下，我们可以使用内嵌汇编来调用cpuid指令。但在64位模式下，VC编译器不支持内嵌汇编。 于是微软提供了Intrinsics函数——编译器会将Intrins... 阅读全文

摘要：一、分解x2APIC_ID摘自《Intel® 64 Architecture Processor Topology Enumeration》中的“Sub ID Extraction Parameters for x2APIC ID”——SMT_ID: CPUID.(EAX=11, ECX=0):EAX[4:0] provides the width parameter to derive a SMT select mask to extract the SMT_IDs of logical processors within the same processor core. The 阅读全文

摘要：有时我们需要编写DOS实模式下的CPU信息诊断程序，但是TurboC++等很多16位C++编译器不支持CPUID指令和32位汇编。于是本文介绍了一种办法，靠内嵌机器码实现了获取CPUID信息。一、CPUID指令简介 CPUID指令是intel IA32架构下获得CPU信息的汇编指令，可以得到CPU类型，型号，厂商信息，商标信息，序列号，缓存等一系列CPU相关的东西。 CPUID指令一般使用使用eax作为输入参数（某些时候会用到ecx），eax、ebx、ecx、edx作为输出参数。例如这样的汇编代码——mov eax, 1cpuid... 以上代码以1为输入参数，执行cpuid后... 阅读全文

摘要：现在多核处理器已经很普及了，市场主流是双核处理器，还有4核、8核等高端产品。而且Intel推广了超线程技术（Hyper-Threading Technology, HTT），可以将一个物理核心模拟为两个逻辑处理器。这一切使得“CPU数量”这一概念变得复杂起来，对于软件开发人员来说，希望能获得物理CPU数、CPU核心数、逻辑CPU数等详细信息。 在Windows平台，可以调用GetLogicalProcessorInformation函数来获取它们的详细信息。一、背景知识 先来明确一下名词——physical processor packages：物理处理器封装个数，即俗称的“物理CPU... 阅读全文

摘要：作者：zyl910 关于SIMD（MMX、SSE、AVX）编程的资料一直很零散，于是我试图进行收集整理，便于随时翻阅学习。而且很多代码是直接用汇编写的，易读性差、难以重用，于是我决定将其统一改写为Intrinsics函数版。一、Instructions函数对照表 在使用Instructions函数时，很多时候会发现MSDN说的不详细，这时只有去翻阅Intel、AMD文档了。但Intel、AMD文档都是按照汇编指令名排序的，查起来不太方便。 而且SIMD指令大多很复杂，文字描述难以详细的解释其功能，唯有伪代码才能精确的解释其功能。但Intel、AMD文档上的伪代码大多很长，不适合随时翻阅。... 阅读全文

摘要：当使用Intrinsics函数来操作SIMD指令集（MMX/SSE/AVX等）时，会面对不同长度的SIMD数据类型，其中又分为多种紧缩格式。为此，我设计了一套SIMD变量命名规范，可以有效的提高代码的可读性。一、SIMD数据类型简介 SIMD数据类型有——__m64：64位紧缩整数（MMX）。__m128：128位紧缩单精度（SSE）。__m128d：128位紧缩双精度（SSE2）。__m128i：128位紧缩整数（SSE2）。__m256：256位紧缩单精度（AVX）。__m256d：256位紧缩双精度（AVX）。__m256i：256位紧缩整数（AVX）。注：紧缩整数包括了8位、16... 阅读全文

摘要：在传统印象中，数字的比较关系只有6种。但在AVX指令集中，Intel一下给出了32种浮点比较谓词，详见下图——（Intel手册：Table 3-9. Comparison Predicate for VCMPPD and VCMPPS Instructions） 为什么会有这么多种比较谓词呢？我为此困惑困惑了很久。 直到最近翻阅了不少资料后，才终于将它们弄懂了。一、浮点数据类型 Intel使用的是IEEE 754规范的浮点数据类型。对于浮点数据类型来说，除了可以存储数字、无穷之外，还可以存储 NaN（not a number。非数）。 NaN（非数）分为两大类——1.QNaN：qu... 阅读全文

摘要：一、测试结果汇总 将前面的测试结果进行汇总，整理为表格（单位是毫秒，数值越小越好）—— 测试f0_iff1_minf2_negf3_sarf4_mmxf5_sseVC6 on 32bit2016206371967237.525.7VC6 on 64bit2028207571868737.125.3VC2010(32) on 32bit17932112512437VC2010(32) on 64bit17162106514437VC2010(64) on 64bit16231997421328C#2010(any) on 32bit192221472471559C#2010(any) on... 阅读全文

摘要：在上一篇测试了MMX指令集，这次我们来测试SSE指令集。说的更精确一点，是测试SSE2指令集。 本篇致力于解决以下问题——1.SSE/SSE2指令集是什么？2.如何阅读Intel/AMD的手册？3.如何运用SSE指令集？如何将MMX代码升级为SSE代码。4.如何在VC++6.0这样的高级语言编译器中使用MMX指令集？一、简介 1999 年 Intel 推出了第 1 代的 SSE（Streaming SIMD Extensions）指令以回击 AMD 的 3DNow! 指令，使用在 Pentium III 处理器上。随后 AMD 在 2001 年 10 月 发布 的 Athlon XP ... 阅读全文