Lỗi phân đoạn khi sử dụng OpenMp và SSE

Question

Tôi chỉ mới bắt đầu thử nghiệm thêm OpenMP vào một số mã SSE.

Chương trình thử nghiệm đầu tiên của tôi SOMETIMES treo trong _mm_set_ps, nhưng hoạt động khi tôi đặt if (0).

Dường như đơn giản, tôi phải bỏ lỡ điều gì đó hiển nhiên. Tôi đang biên soạn với gcc -g -fopenmp -march = Core2 -pthreads

#include <stdio.h> 
    #include <stdlib.h> 
    #include <immintrin.h> 

    int main() 
    { 
    #pragma omp parallel if (1) 
    { 
    #pragma omp sections 
     { 
    #pragma omp section 
      { 
       __m128 x1 = _mm_set_ps (1.1f, 2.1f, 3.1f, 4.1f); 
      } 
    #pragma omp section 
      { 
       __m128 x2 = _mm_set_ps (1.2f, 2.2f, 3.2f, 4.2f); 
      } 
     } // end omp sections 
    } //end omp parallel 

    return 0; 
    } 

Answer 1

Đây là lỗi trong quá trình triển khai OpenMP. Tôi đã gặp vấn đề tương tự trong gcc trên Windows (MinGW). -mstackrealign tùy chọn dòng lệnh đã giải quyết được sự cố của tôi. Điều này thêm một lệnh vào phần mở đầu của mọi hàm để căn chỉnh lại ngăn xếp tại ranh giới 16-byte. Tôi đã không nhận thấy bất kỳ hình phạt hiệu suất nào. Bạn cũng có thể thử thêm __attribute__ ((force_align_arg_pointer)) vào một khai báo chức năng, sẽ thực hiện tương tự, nhưng chỉ cho một hàm cụ thể. Bạn có thể phải đặt mã SSE trong một hàm riêng biệt mà sau đó bạn gọi từ hàm bằng #pragma omp, để ngăn xếp có cơ hội được sắp xếp lại.

Tôi đã ngừng gặp sự cố khi tôi chuyển sang biên dịch cho mục tiêu 64 bit (MinGW64, chẳng hạn như TDM GCC bản dựng).

Tôi đang phát với hướng dẫn AVX yêu cầu căn chỉnh 32 byte nhưng GCC không hỗ trợ cửa sổ đó. Điều này buộc tôi phải sửa mã lắp ráp được sản xuất bằng cách sử dụng một tập lệnh python, nhưng nó hoạt động.

Answer 2

Tôi ngửi thấy truy cập bộ nhớ unaligned. Mã duy nhất của nó giống như vậy có thể phát nổ (giả sử rằng là mã duy nhất ở đó là). Để điều đó xảy ra, các thanh ghi XMM sẽ không được sử dụng mà là bộ nhớ ngăn xếp, nó chỉ liên kết với 4 byte, tôi đoán là mã omp đang làm rối tung sự sắp xếp của chồng.