OpenCL - работа с памятью GPU

@DENIS94 · Регистрация: 12.04.2013

Author24 — интернет-сервис помощи студентам

Кто знает OpenCL? Откликнитесь!

У меня тут необъяснимые проблемы при обращении к динамическим данным по указателю в ядре (__kernel). Возвращается вообще полный бред

@DENIS94 · 23.01.2015, 21:35 **[ТС]**

Сообщение от castaway

Что еще уточнить?

Да вроде как нет

Теперь все стало ясно. Спасибо)

@snake32 · 24.01.2015, 03:31

DENIS94,
1) не понял зачем нужен OpenCL если ядро запускается в 1 поток? Ну да ладно, он тоже должен работать.
2) описал выделения памяти под 2 массива m_rkw и ms_out. Так же заполнил ms_out. Однако в ядре 3 массива. Что там с ms_in? Память то выделена?
3) почти каждая ф-ия OpenCL возвращает код ошибки. Обязательно проверяйте их все. Особенно на ранних стадиях освоения OpenCL.

@DENIS94 · 24.01.2015, 14:37 **[ТС]**

Сообщение от snake32

1) не понял зачем нужен OpenCL если ядро запускается в 1 поток? Ну да ладно, он тоже должен работать.
2) описал выделения памяти под 2 массива m_rkw и ms_out. Так же заполнил ms_out. Однако в ядре 3 массива. Что там с ms_in? Память то выделена?

1) Тестирую. потом будут запуски в больших измерениях.
2) Я писал, что ms_in пока не используется. Под него память выделяется. Она по размеру точно такая же как и под ms_out. По задумке в ms_in с хоста копируются данные при создании буфера. Потом блок шифруется при использовании раундовых ключей m_rkw и все записывается в ms_out.

@DENIS94 · 25.01.2015, 18:47 **[ТС]**

Я наконец то нашел в чем была проблема!

Не по теме:

И по черному проматерился из за такой глупости!

Я не знаю как именно воспринимает типы данных компилятор OpenCL. Но походу unsigned long int и unsigned int для него к рай разные типы. Я поменял все типы указателей с unsigned long int на unsigned int и все сразу же заработало как полагается.

C++

__kernel void runKerEncData_L128_R10(__global unsigned char * ms_in, __global unsigned char * ms_out, __global unsigned int * m_rkw)
{
    union process_block
    {
        __private unsigned int  ms_ul[4];
        __private unsigned char ms_uc[16];
    } __private block_u, block_y;
    union ms_conv
    {
        __global unsigned char * ms_uc;
        __global unsigned int * ms_ul;
    } __private msin_conv, msout_conv;
    
    __private int ID_BLOCK = get_global_id(0) * 16;
 
    msin_conv.ms_uc  = &ms_in[ID_BLOCK];
    msout_conv.ms_uc = &ms_out[ID_BLOCK];
 
    //................
}

Вообще странно все это. Для меня это был просто закон(!). unsigned long int = 4 байта. Ни больше ни меньше. Видимо OpenCL захапывал все 8 или тока 2.

даже строчка: std::cout « sizeof(unsigned int) « "\n" « sizeof(unsigned long int); в MVS 2013 выдает:
4
4

В общем, будьте внимательнее с типами данных при работе с этим языком. Там не всегда все так как хотелось бы.

@castaway · 25.01.2015, 19:14

Сообщение от DENIS94

Но походу unsigned long int и unsigned int для него к рай разные типы.

Насколько мне известно, в OpenCL нет типа unsigned long int.
Открой для себя CheatSheet. Полезная штука)

Сообщение от DENIS94

даже строчка: std::cout « sizeof(unsigned int) « "\n" « sizeof(unsigned long int); в MVS 2013 выдает

Я бы не стал сравнивать встроенные типы MSVS и встроенные типы OpenCL. У них всё-таки разные стандарты.

@DENIS94 · 25.01.2015, 19:38 **[ТС]**

Сообщение от castaway

Открой для себя CheatSheet. Полезная штука)

Не открывается)

Сообщение от castaway

Насколько мне известно, в OpenCL нет типа unsigned long int.

И я просто unsigned long пробовал. То же не работало..

@DENIS94 · 25.01.2015, 19:42 **[ТС]**

Сообщение от DENIS94

И я просто unsigned long пробовал. То же не работало..

Пфф.. оно и понятно почему

>> скрин PDF

В общем язык новый для меня. И придется еще пару сотен граблей собрал

@castaway · 25.01.2015, 19:43

Сообщение от DENIS94

Не открывается)

Вот. Или набери в гугле "opencl cheatsheet", там будут ссылки на www.khronos.org

Сообщение от DENIS94

И я просто unsigned long пробовал. То же не работало..

unsigned long в OpenCL имеет размер 64 бита, unsigned int - 32.

Сообщение от DENIS94

Пфф.. оно и понятно почему

Да да да..

@snake32 3460 / 1648 / 236 Регистрация: 26.02.2009 Сообщений: 8,051 Записей в блоге: 5
	24.01.2015, 03:31	22
	DENIS94, 1) не понял зачем нужен OpenCL если ядро запускается в 1 поток? Ну да ладно, он тоже должен работать. 2) описал выделения памяти под 2 массива m_rkw и ms_out. Так же заполнил ms_out. Однако в ядре 3 массива. Что там с ms_in? Память то выделена? 3) почти каждая ф-ия OpenCL возвращает код ошибки. Обязательно проверяйте их все. Особенно на ранних стадиях освоения OpenCL. 0

@DENIS94 24 / 24 / 6 Регистрация: 12.04.2013 Сообщений: 122
	25.01.2015, 19:38 [ТС]	26
	Сообщение от castaway Открой для себя CheatSheet. Полезная штука) Не открывается) Сообщение от castaway Насколько мне известно, в OpenCL нет типа unsigned long int. И я просто unsigned long пробовал. То же не работало.. 0

@DENIS94 24 / 24 / 6 Регистрация: 12.04.2013 Сообщений: 122
	25.01.2015, 19:42 [ТС]	27
	Сообщение от DENIS94 И я просто unsigned long пробовал. То же не работало.. Пфф.. оно и понятно почему >> скрин PDF В общем язык новый для меня. И придется еще пару сотен граблей собрал Миниатюры 0

@DENIS94 24 / 24 / 6 Регистрация: 12.04.2013 Сообщений: 122
		1
	OpenCL - работа с памятью GPU 23.01.2015, 17:16. Показов 6091. Ответов 27 Метки нет (Все метки) Кто знает OpenCL? Откликнитесь! У меня тут необъяснимые проблемы при обращении к динамическим данным по указателю в ядре (__kernel). Возвращается вообще полный бред 1

@DENIS94 24 / 24 / 6 Регистрация: 12.04.2013 Сообщений: 122
	23.01.2015, 21:35 [ТС]	21
	Сообщение от castaway Что еще уточнить? Да вроде как нет Теперь все стало ясно. Спасибо) 1

@DENIS94 24 / 24 / 6 Регистрация: 12.04.2013 Сообщений: 122
	24.01.2015, 14:37 [ТС]	23
	Сообщение от snake32 1) не понял зачем нужен OpenCL если ядро запускается в 1 поток? Ну да ладно, он тоже должен работать. 2) описал выделения памяти под 2 массива m_rkw и ms_out. Так же заполнил ms_out. Однако в ядре 3 массива. Что там с ms_in? Память то выделена? 1) Тестирую. потом будут запуски в больших измерениях. 2) Я писал, что ms_in пока не используется. Под него память выделяется. Она по размеру точно такая же как и под ms_out. По задумке в ms_in с хоста копируются данные при создании буфера. Потом блок шифруется при использовании раундовых ключей m_rkw и все записывается в ms_out. 0

@castaway 4986 / 3093 / 456 Регистрация: 10.11.2010 Сообщений: 11,169 Записей в блоге: 10
	25.01.2015, 19:14	25
	Сообщение от DENIS94 Но походу unsigned long int и unsigned int для него к рай разные типы. Насколько мне известно, в OpenCL нет типа unsigned long int. Открой для себя CheatSheet. Полезная штука) Сообщение от DENIS94 даже строчка: std::cout « sizeof(unsigned int) « "\n" « sizeof(unsigned long int); в MVS 2013 выдает Я бы не стал сравнивать встроенные типы MSVS и встроенные типы OpenCL. У них всё-таки разные стандарты. 0

@castaway 4986 / 3093 / 456 Регистрация: 10.11.2010 Сообщений: 11,169 Записей в блоге: 10
	25.01.2015, 19:43	28
	Сообщение от DENIS94 Не открывается) Вот. Или набери в гугле "opencl cheatsheet", там будут ссылки на www.khronos.org Сообщение от DENIS94 И я просто unsigned long пробовал. То же не работало.. unsigned long в OpenCL имеет размер 64 бита, unsigned int - 32. Сообщение от DENIS94 Пфф.. оно и понятно почему Да да да.. 1