Intel® C++ Compiler 16.0 User and Reference Guide

_mm512_extload_epi64/ _mm512_mask_extload_epi64

Loads/broadcasts/converts int64 vector. Corresponding instruction is VMOVDQA64. This intrinsic only applies to Intel® Many Integrated Core Architecture (Intel® MIC Architecture).

Syntax

Without Mask

extern __m512i __cdecl _mm512_extload_epi64(void const* mt, _MM_UPCONV_EPI64_ENUM conv, _MM_BROADCAST64_ENUM bc, int hint);

With Mask

extern __m512i __cdecl _mm512_mask_extload_epi64(__m512i v1_old, __mmask8 k1, void const* mt, _MM_UPCONV_EPI64_ENUM conv, _MM_BROADCAST64_ENUM bc, int hint);

Arguments

v1_old

 Source vector that retains old values of the destination vector; the resulting vector gets corresponding elements from v1_old for zero mask bits

k1

 Writemask; only those elements of the source vectors with corresponding bit set to '1' in the k1 mask are computed and stored in the result; elements in the result vector corresponding to zero bit in k1 are copied from corresponding elements of vector v1_old

conv

Type of upconversion, which can be one of the following:

  • _MM_UPCONV_EPI64_NONE - no conversion

bc

Type of broadcast, which can be one of the following:

  • _MM_BROADCAST64_NONE - identity swizzle/convert
  • _MM_BROADCAST_1X8 - broadcast x 8 ( aaaa aaaa )
  • _MM_BROADCAST_4X8 - broadcast x 2 ( dcba dcba )

mt

memory address from where loading occurs

hint

Hint that indicates to the processor that the data is non-temporal. Takes the value 0 or 1, where:

  • _MM_HINT_NONE = 0
  • _MM_HINT_NT = 1 (Load is non-temporal)

Description

Depending on the bc parameter, loads one (bc=_MM_BROADCAST_1X8), four (bc=_MM_BROADCAST_4X8), or eight (bc=_MM_BROADCAST64_NONE) elements at memory address mt, converts them to int64 values, and returns the result in a int64 vector. The type and the size of elements read from memory depend on the parameter conv .

The masked variant has two additional arguments:v1_old and k1. Only those elements with the corresponding bit set to one in vector mask k1 are computed. Elements in resulting vector with the corresponding bit clear in k1 obtain values from the v1_old vector.

Note

This intrinsic requires the memory address mt to be aligned to the data size granularity dictated by the bc and conv parameters. So the minimum required alignment is 8, 32, or 64 bytes depending on the broadcast (1x8, 4x8, none).

Returns

Returns the result of the load/broadcast/convert operation.

Parent topic: Load Intrinsics