bộ nhớ vật lý trên các thiết bị AMD: cục bộ và riêng

Question

Tôi đang viết một thuật toán trong OpenCL, trong đó tôi cần mọi đơn vị công việc để ghi nhớ một phần dữ liệu hợp lý, nói điều gì đó giữa long[70] và long[200] hoặc hạt nhân.

Thiết bị AMD gần đây có 32 bộ nhớ KiB __local, tức là (cho số lượng dữ liệu nhất định cho mỗi hạt nhân) đủ để lưu trữ thông tin cho 20-58 đơn vị làm việc. Tuy nhiên, từ những gì tôi hiểu từ kiến ​​trúc (và đặc biệt là từ this drawing), mỗi lõi của trình đổ bóng cũng có một lượng bộ nhớ riêng. Tuy nhiên tôi không tìm thấy kích thước của nó.

Bất cứ ai có thể cho tôi biết làm thế nào để tìm ra bao nhiêu bộ nhớ riêng mỗi hạt nhân có?

Tôi đặc biệt tò mò về HD7970, vì tôi dự định mua một số trong số này sớm.

Edit: Giải quyết vấn đề, câu trả lời là here trong phụ lục D.

Answer 1

Câu trả lời đã được đưa ra bởi người dùng tài năng trong các ý kiến, vì vậy tôi sẽ viết nó trong một câu trả lời mới ở đây để đóng câu hỏi.

Các giá trị này có thể được tìm thấy trong Phụ lục D của Hướng dẫn lập trình AMD APP OpenCL http://developer.amd.com/sdks/amdappsdk/assets/amd_accelerated_parallel_processing_opencl_programming_guide.pdf (tài liệu tương tự tồn tại cho nVidia). Rõ ràng một thanh ghi là 128 bit (4x32) cho các thiết bị AMD và có 16384 thanh ghi cho tất cả các thiết bị cao cấp hiện đại, vì vậy đó là một 256KB đáng kể cho mỗi đơn vị tính toán.

Answer 2

Tôi nghĩ rằng bạn đang tìm kiếm bộ nhớ __local. Đó là những gì 32KB lưu trữ dữ liệu cục bộ đang đề cập đến. Tôi không nghĩ rằng bạn có thể thăm dò ý kiến ​​thiết bị để có được số lượng bộ nhớ riêng.

Bạn có thể truyền tham số NULL * cl_mem dài để cấp phát bộ nhớ. Tôi nghĩ tốt nhất là sử dụng một lượng bộ nhớ tĩnh cho mỗi WI. Giả sử rằng dài [200] sẽ được yêu cầu cho mỗi mục công việc, bạn sẽ sử dụng mã dưới đây. Nó cũng sẽ là một ý tưởng tốt để chia công việc thành các nhóm có cùng yêu cầu bộ nhớ (hoặc tương tự), để tận dụng tối đa bộ nhớ LDS.

void __kernel(__local long* localMem, const int localMemPerItem 
     //more args... 
     ) 
{ 
    //host has 'passed' localMemPerItem*get_local_size() long values in as locamMem 
    //this work item has access to all of it, but can choose to restrict 
    //itself to only the portion it needs. 
    //work group size will be limited to CL_DEVICE_LOCAL_MEM_SIZE/(8*localMemPerItem) 
    int startIndex=localMemPerItem*get_local_id(0); 
    //use localMem[startIndex+ ... ] 
} 

Answer 3

Để trả lời như thế nào lớn là đăng ký tập tin trong thẻ loạt 79xx, vì nó dựa trên kiến ​​trúc GCN nó là 64KB theo hình ảnh trong Anandtech: http://www.anandtech.com/print/5261

Để trả lời câu hỏi của bạn làm thế nào để tìm hiểu cách thức nhiều bộ nhớ mỗi hạt nhân sử dụng .. bạn có thể xem chạy AMD APP Profiler trên hạt nhân của bạn, nó cho bạn biết trong phần dung lượng hạt nhân bao nhiêu không gian được sử dụng bởi hạt nhân.