Арифметика пустого указателя OpenCL - странное поведение

Для указателей void* не существует арифметики указателей. Используйте указатели char* для выполнения побайтовых вычислений указателя.

Или намного лучше: используйте тип real, на который указывает указатель, и не умножайте смещения. Просто напишите vertex[index+base], предполагая, что vertex указывает на ваш тип, содержащий 28 байт данных.

Соображения производительности. Выровняйте атрибуты вершин по степени двойки для объединенного доступа к памяти. Это означает, что после каждой записи вершины необходимо добавить 4 байта заполнения. Чтобы сделать это автоматически, используйте float8 в качестве типа вершины, если все ваши атрибуты являются значениями с плавающей запятой. Я предполагаю, что вы работаете с позицией и данными нормалей или чем-то подобным, поэтому может быть хорошей идеей написать пользовательскую структуру, которая инкапсулирует оба вектора удобным и понятным способом:

// Defining a type for the vertex data. This is 32 bytes large.
// You can share this code in a header for inclusion in both OpenCL and C / C++!
typedef struct {
    float4 pos;
    float4 normal;
} VertexData;

// Example kernel
__kernel void computeNormalKernel(__global VertexData *vertex, uint base) {
    uint index = get_global_id(0);
    VertexData thisVertex = vertex[index+base];   // It can't be simpler!
    thisVertex.normal = computeNormal(...);       // Like you'd do it in C / C++!
    vertex[index+base] = thisVertex;              // Of couse also when writing
}

Примечание. Этот код не работает с вашим шагом 28, если вы просто измените один из float4 на float3, поскольку float3 также потребляет 4 числа с плавающей запятой памяти. Но вы можете написать это так, что не добавит заполнения (но обратите внимание, что это будет штрафовать пропускную способность доступа к памяти):

typedef struct {
    float pos[4];
    float normal[3];  // Assuming you want 3 floats here
} VertexData;