int64_t Zeiger auf AVX2 intrinsisch _m256i

Question

Hallo Ich habe ein seltsames Problem mit AVX2 intrinsics. Ich erstelle einen Zeiger auf einen _m256i Vektor mit einer int64_t * Besetzung. Ich weise dann einen Wert zu, indem ich den Zeiger dereferenziere. Das Seltsame ist, dass der Wert in der Vektorvariablen nicht beobachtet wird, es sei denn, ich führe ein paar Cout-Anweisungen danach aus. Der Zeiger und der Vektor haben die gleiche Speicheradresse, und bei der Dereferenzierung erzeugt der Zeiger den richtigen Wert, der Vektor jedoch nicht. Was vermisse ich?

// Vector Variable 
__m256i R_A0to3 = _mm256_set1_epi32(0xFFFFFFFF); 

int64_t *ptr = NULL; 
for(int m=0; m<4; m++){ 
    // Cast pointer to vector type 
    ptr = (int64_t*)&R_A0to3; 

    cout<<"ptr_ADDRESS:  "<<ptr<<endl; 
    cout<<"&R_A0to3_ADDRESS: "<<&R_A0to3<<endl; 

    // access 
    ptr[m] = (int64_t) m_array[m]; 

    // generic function that prints out register 
    print_mm256_reg<int64_t>(R_A0to3, "R_A0to3"); 
    cout<<"m_array: "<< m_array[m]<<std::ends; 

    // Additional print statements 
    cout<<"ptr[m]: "<< ptr[m]<<std::endl; 
    cout<<"ptr[0]: "<< ptr[0]<<std::endl; 
    cout<<"ptr[1]: "<< ptr[1]<<std::endl; 
    cout<<"ptr[2]: "<< ptr[2]<<std::endl; 
    cout<<"ptr[3]: "<< ptr[3]<<std::endl; 
    print_mm256_reg<int64_t>(R_A0to3, "R_A0to3"); 
} 

---

Output: 
ptr_ADDRESS  0x7ffd9313e880 
&R_A0to3_ADDRESS 0x7ffd9313e880 
m_array: 8 
printing reg - R_C0to3 -1| -1| -1| -1| 
printing reg - R_D0to3 -1| -1| -1| -1| 

Output with Additional print statements: 
ptr_ADDRESS  0x7ffd36359e20 
&R_A0to3_ADDRESS 0x7ffd36359e20 
printing reg - R_A0to3  -1| -1| -1| -1| 
m_array: 8 

ptr[0]: 8 
ptr[1]: -1 
ptr[2]: -1 
ptr[3]: -1 
printing reg - R_A0to3  8| -1| -1| -1| 

Answer 1

Ich schlage vor, die _mm256_extract_epi64 und _mm256_insert_epi64 intrinsics verwenden, wenn Sie gelegentlich Zugriff auf einzelne Elemente benötigen. Wenn Sie auf alle Elemente aus dem Vektor zugreifen müssen, sollten Sie die Dateien _mm256_store_si256 und _mm256_lddqu_si256 zum Speichern und Laden verwenden. Diese intrinsischen Eigenschaften sind weniger auf ein undefiniertes Verhalten angewiesen und sie sind transparent hinsichtlich der erzeugten Maschinenanweisungen (und somit bezüglich der Leistung).