OpenCL 1.1

OpenCL 1.1 to kolejna wersja tego standardu, wprowadzająca ulepszenia w zarządzaniu pamięcią i synchronizacją wątków.

OpenCL 1.1 jako standard obliczeń heterogenicznych

OpenCL 1.1 to wersja standardu Khronos Group przeznaczona do wykonywania obliczeń równoległych na różnych typach urządzeń. Program OpenCL może korzystać z procesora CPU, procesora graficznego GPU albo innego akceleratora obliczeniowego, jeżeli dany sprzęt udostępnia zgodną implementację sterownika. Standard nie jest sterownikiem konkretnej karty graficznej ani biblioteką przypisaną do jednego producenta. Określa interfejs programistyczny, model wykonania oraz zestaw funkcji dostępnych dla aplikacji i jąder obliczeniowych.

W OpenCL 1.1 aplikacja działa w modelu platformy i urządzeń. Platforma reprezentuje implementację dostarczoną przez producenta, natomiast urządzenie jest konkretnym procesorem lub akceleratorem widocznym w tej platformie. Program tworzy kontekst, kolejkę poleceń, obiekty pamięci oraz jądra, a następnie umieszcza operacje w kolejce. Jądro, czyli funkcja wykonywana równolegle przez wiele elementów roboczych, może przetwarzać duże tablice danych, obrazy, macierze albo inne regularne struktury.

Zmiany w pamięci i synchronizacji względem OpenCL 1.0

Jedną z istotnych możliwości OpenCL 1.1 jest tworzenie podbuforów za pomocą funkcji clCreateSubBuffer. Podbufor wskazuje określony fragment istniejącego obiektu bufora, dzięki czemu aplikacja może przekazać do jądra tylko wybrany zakres danych bez tworzenia całej kopii w pamięci. Region podbufora musi być opisany offsetem i rozmiarem zgodnym z ograniczeniami urządzenia, w tym z wymaganym wyrównaniem. Sam podbufor pozostaje powiązany z buforem nadrzędnym, więc operacje na pamięci nadal podlegają regułom dostępu oraz synchronizacji OpenCL.

OpenCL 1.1 rozszerza także obsługę operacji prostokątnych na buforach. Funkcje takie jak clEnqueueReadBufferRect, clEnqueueWriteBufferRect i clEnqueueCopyBufferRect pozwalają opisywać fragmenty danych za pomocą offsetów, wymiarów oraz parametrów kroku wiersza i warstwy. Jest to przydatne przy przenoszeniu części obrazu lub wielowymiarowej tablicy, gdy dane w pamięci mają określony układ. Dzięki temu nie trzeba zawsze układać całego fragmentu w osobny, liniowy bufor po stronie hosta.

Wersja 1.1 wprowadza również zdarzenia użytkownika oraz mechanizm wywołań zwrotnych dla zdarzeń. Zdarzenie użytkownika może zostać utworzone przez aplikację i oznaczone jako zakończone dopiero po spełnieniu warunku zewnętrznego wobec kolejki OpenCL. Funkcja clSetEventCallback umożliwia zarejestrowanie funkcji wywoływanej przy zmianie stanu zdarzenia, na przykład po zakończeniu polecenia albo wystąpieniu błędu. Takie mechanizmy pozwalają budować przepływ pracy bez ciągłego blokowania wątku hosta przez synchroniczne oczekiwanie.

Jądra, typy wektorowe i zgodność implementacji

Jądra OpenCL 1.1 są pisane w języku opartym na C99, z rozszerzeniami przeznaczonymi do obliczeń równoległych. Kod jądra korzysta między innymi z identyfikatorów elementu roboczego, grup roboczych, pamięci lokalnej i pamięci prywatnej. Aplikacja uruchamia jądro przez funkcję clEnqueueNDRangeKernel, podając wymiar przestrzeni indeksów oraz lokalny i globalny rozmiar pracy. Rozmiary te muszą odpowiadać ograniczeniom konkretnego urządzenia, dlatego aplikacja powinna odczytywać właściwości przez zapytania takie jak clGetDeviceInfo, zamiast zakładać stałe wartości.

OpenCL 1.1 formalizuje obsługę trójelementowych typów wektorowych, takich jak float3, int3 i uint3. W praktyce rozmiar wektora trójelementowego w pamięci może podlegać regułom wyrównania właściwym dla wektora czteroelementowego. Z tego powodu kod hosta i kod jądra muszą zgodnie interpretować rozmiary oraz układ struktur. Bezpośrednie założenie, że float3 zawsze zajmuje dokładnie trzy razy po cztery bajty, może prowadzić do błędów przy kopiowaniu struktur między pamięcią hosta i urządzenia.

Zgodność z OpenCL 1.1 nie oznacza jednak identycznej wydajności na każdym komputerze. Sterownik może obsługiwać różne typy urządzeń, formaty obrazów, rozmiary pamięci oraz zakresy rozmiarów grup roboczych. Aplikacja powinna sprawdzać wersję platformy, wersję urządzenia, listę rozszerzeń i wartości limitów. Przy diagnozowaniu problemu ważne jest rozdzielenie błędu aplikacji od braku funkcji w sterowniku: nieprawidłowy kontekst, niezgodny typ urządzenia, błędny rozmiar bufora albo naruszenie wyrównania mogą skutkować kodem błędu zwróconym przez funkcję OpenCL.

OpenCL 1.1 w praktyce serwisowej komputera

Problemy z aplikacją wykorzystującą OpenCL 1.1 mogą objawiać się błędem podczas tworzenia kontekstu, brakiem urządzenia na liście, nieudanym zbudowaniem programu albo nieprawidłowym wynikiem obliczeń. W pierwszej kolejności sprawdza się, czy system widzi właściwy sterownik, czy biblioteka implementacji jest dostępna oraz czy aplikacja wybiera urządzenie zgodne z wymaganiami. Następnie można porównać wersję platformy i urządzenia, sprawdzić komunikat kompilatora jądra oraz przeanalizować kolejność operacji pamięci i zdarzeń. Sam fakt obecności sterownika graficznego nie gwarantuje obsługi wszystkich funkcji wymaganych przez aplikację.

W przypadku komputera, na którym program OpenCL działa niestabilnie, znaczenie mają również błędy pamięci, przegrzewanie podzespołów, uszkodzenie sterownika albo niezgodność aplikacji z architekturą urządzenia. Diagnostyka powinna rozróżniać awarię sprzętu od problemu programowego. Pomocne jest sprawdzenie działania na innym urządzeniu OpenCL, odczyt kodów zwracanych przez funkcje API oraz weryfikacja, czy błąd występuje przy konkretnym jądrze, buforze lub operacji synchronizacji. Warszawskie Pogotowie Komputerowe wykonuje profesjonalną naprawę laptopów, komputerów PC i ich podzespołów.