Visible to Intel only — GUID: GUID-48018B52-8890-406F-91C0-AD64306B2110
Visible to Intel only — GUID: GUID-48018B52-8890-406F-91C0-AD64306B2110
vector_variant
Specifies a vector variant function that corresponds to its original C/C++ scalar function. This vector variant function can be invoked under vector context at call sites.
Windows* OS: __declspec(vector_variant(clauses)) |
Linux* OS: __attribute__((vector_variant(clauses))) |
clauses |
Is the following: implements clause, in the form implements (<function declarator>) [, <simd-clauses>]), where function declarator is the original scalar function, and simd-clauses is one or more of the clauses allowed for the vector attribute. The simd-clauses are optional. |
This attribute provides a means for programmers to describe the association between the vector variant function and its corresponding scalar function. The compiler will use the vector variant to replace the scalar call for a vectorized loop.
The following are restrictions for this attribute:
A vector variant function can have only one vector_variant annotation.
A vector variant annotation can have only one implements clause.
A vector variant annotation applies to only one vector variant function, which must not have both mask and nomask clauses specified. It can be specified with either mask or nomask; the default is nomask.
- A vector variant function should have the __regcall attribute.
If the user-defined vector variant function is a variant with mask, the mask argument should be the last argument.
Example
The following shows an example of a vector variant function:
#include <immintrin.h> __declspec(noinline) float MyAdd(float* a, int b) { return *a + b; } __declspec(vector_variant(implements(MyAdd(float *a, int b)), linear(a), vectorlength(8), nomask, processor(core_2nd_gen_avx))) __m256 __regcall MyAddVec(float* v_a, __m128i v_b, __m128i v_b2) { __m256i t96 = _mm256_castsi128_si256(v_b); __m256i tmp = _mm256_insertf128_si256(t96, v_b2, 1); __m256 t95 = _mm256_cvtepi32_ps(tmp); return _mm256_add_ps(*((__m256*)v_a), t95); } float x[2000], y[2000]; float foo(float y[]) { #pragma omp simd for (int k=0; k< 2000; k++) { x[k] = MyAdd(&y[k], k); } return x[0] + x[1999];
If the return value contains more than one register, the following technique can be used for the correct definition of the function:
#include <immintrin.h> typedef struct { __m256d r1; __m256d r2; } __m256dx2; __declspec(noinline) double MyAdd(double* a, int b) { return *a + b; } __declspec(vector_variant(implements(MyAdd(double *a, int b)), linear(a), vectorlength(8), nomask, processor(core_2nd_gen_avx))) __m256dx2 __regcall MyAddVec(double* v_a, __m128i v_b, __m128i v_b2) { __m256d t1 = _mm256_cvtepi32_pd(v_b); __m256d t2 = _mm256_cvtepi32_pd(v_b2); __m256dx2 ret; ret.r1 = _mm256_mul_pd(t1,*((__m256d*)v_a)); ret.r2 = _mm256_mul_pd(t2,*(((__m256d*)v_a)+1)); return ret; } __declspec(align(32)) double x[2000], y[2000]; double foo(double* y) { #pragma omp simd for (int k=0; k< 2000; k++) { x[k] = MyAdd(y, k); y++; } return x[0] + x[1999]; }