Intel® C++ Compiler 16.0 User and Reference Guide

_mm512_extloadunpackhi_ps/ _mm512_mask_extloadunpackhi_ps

Loads high 64-byte aligned portion of unaligned doubleword stream, unpacks mask-enabled elements that fall in that portion, and stores those elements in float32 vector. Corresponding instruction is VLOADUNPACKHD. This intrinsic only applies to Intel® Many Integrated Core Architecture (Intel® MIC Architecture).

Syntax

Without Mask

extern __m512 __cdecl _mm512_extloadunpackhi_ps(__m512 v1_old, void const* mt, _MM_UPCONV_PS_ENUM conv, int hint);

With Mask

extern __m512 __cdecl _mm512_mask_extloadunpackhi_ps(__m512 v1_old, __mmask16 k1, void const* mt, _MM_UPCONV_PS_ENUM conv, int hint);

Arguments

v1_old

source vector that contains initial values for the destination vector

k1

writemask

mt

memory address from where loading occurs

conv

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

  • _MM_UPCONV_PS_NONE - no conversion
  • _MM_UPCONV_PS_FLOAT16 - sint8 => float32
  • _MM_UPCONV_PS_UINT8 - uint8 => float32
  • _MM_UPCONV_PS_SINT8 - sint8 => float32
  • _MM_UPCONV_PS_UINT16 - uint16 => float32
  • _MM_UPCONV_PS_SINT16 - sint16 => float32

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

The high-64-byte-aligned portion of the byte/word/doubleword stream starting at the element-aligned address (mt − 64) is loaded, converted, and expanded into the writemask-enabled elements of resulting doubleword vector, for which the initial values are copied from v1_old vector. The number of set bits in the writemask determines the length of the converted doubleword stream, as each doubleword is mapped to exactly one of the doubleword elements in the resulting vector, skipping over writemasked elements of the resulting vector.

This function only transfers those converted doublewords (if any) in the stream that occur at or after the first 64-byte-aligned address following (mt − 64) (that is, in the high cache line of the memory stream for the current implementation). Elements in the resulting vector that do not map to those stream doublewords are left unchanged (taken from v1_old).

Returns

Returns the result of the load operation.

Parent topic: Load Intrinsics