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

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

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

Кто знает 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++
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
__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

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

Да да да..

Новые блоги и статьи Все статьи Все блоги /
Расчёт периметра прямоугольника по координатам вершин Maks 18.07.2026 Решение задачи по прикладной информатике средствами 1С. Задача: Вычислить периметр прямоугольника, заданного координатами своих вершин на плоскости. Решение: Создан документ со следующими. . .	Подсчёт частоты трёхбуквенных слов в тексте Maks 18.07.2026 Решение задачи по прикладной информатике средствами 1С. Задача: Выясните, сколько раз в предложенном тексте встречается каждое трехбуквенное слово. Решение: Создан документ с единственным. . .	Сумма и количество положительных элементов в чётных строках массива Maks 18.07.2026 Решение задачи по прикладной информатике средствами 1С. Задача: Вычислить сумму и количество положительных элементов массива, расположенных в четных строках. Решение: Создан документ с. . .	Поиск произведения положительных чётных чисел в последовательности Maks 18.07.2026 Решение задачи по прикладной информатике средствами 1С. Задача: Дана произвольная последовательность целых чисел. Найти произведение положительных четных чисел данной последовательности. . . .
Обработка трёх чисел: утроение и возведение в степень Maks 18.07.2026 Решение задачи по прикладной информатике средствами 1С. Задача: Даны три действительных числа. Утроить те из них, значения которых неотрицательны, и возвести в четвертую степень отрицательные. . . .	Расчёт стоимости яблок по весу Maks 18.07.2026 Решение задачи по прикладной информатике средствами 1С. Задача: Написать программу вычисления стоимости некоторого количества (по весу) яблок. Решение: Создан документ, с табличной частью. . .	сукцессия 30. Фосфорный и азотный замки по "честному" закону лимитирования Либиха anaschu 16.07.2026 Основные достижения за последние дни 1. Механизм отложенного высвобождения фосфора Добавлен специальный пул для медленного разложения меланизированных гиф ЕСМ Реализована разная скорость. . .	Запрет пометки на удаление и отмены проведения Maks 16.07.2026 Алгоритм из решения ниже реализован на нетиповом документе "ПутевойЛист" разработанного в КА2. Задача: запретить помечать на удаление и отменять проведения путевого листа при условии, если он сдан. . .

@DENIS94 24 / 24 / 6 Регистрация: 12.04.2013 Сообщений: 122

	OpenCL - работа с памятью GPU 23.01.2015, 17:16. Показов 6934. Ответов 27 Метки нет (Все метки) Кто знает OpenCL? Откликнитесь! У меня тут необъяснимые проблемы при обращении к динамическим данным по указателю в ядре (__kernel). Возвращается вообще полный бред 1

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