Ecrire un driver graphique de base. (Juste pour le fun)

Version imprimable

23/05/2015, 07h42
Invité

Ecrire un driver graphique de base. (Juste pour le fun)

Salut, je souhaiterai écrire un driver graphique de base, juste pour le fun, une technologie similaire à OpenCL avec juste des allocations de buffers, du transfert de données, etc...

Mais je ne sais pas par ou commencer.

Comme d'habitude je n'ai pas envie de rentrer dans un code existant volumineux, surtout si celui-ci n'est pas documenté.

Car, j'ai vraiment du mal de trouver de tutoriels C++ là dessus d'autant plus que cela dépend fort de chaque modèle de carte graphique.
23/05/2015, 10h33
Christophe

OpenCL n'est pas un driver graphique mais une API.

Que veux-t faire exactement ?
23/05/2015, 21h25
Invité

De la programmation au niveau de la carte graphique, mais pas au niveau de l'api, à plus bas niveau. (Comme on le fait pour le CPU quoi!)

Le problème des apis est quelle ne sont pas toujours supportée par les cartes graphiques. (Contrairement à un langage qui lui, l'est, comme par exemple, le c++ mais ce n'est que pour le CPU. :/)

J'ai l'impression qu'il faudra que j'attente la sortie de VULKAN et que je m'achète un troisième PC. :/
24/05/2015, 09h32
LittleWhite

Bonjour,

Citation:

De la programmation au niveau de la carte graphique

On ne peux pas programmer dans les cartes graphiques. Le seul code que nous pouvons exécuter sur une carte graphique est celui des shaders (GLSL/HLSL), ou des kernels (OpenCL/CUDA/...).

Au final, les cartes graphiques sont un bloc opaque et on ne peux pas y accéder facilement.
La piste que je vous donnerai, qui est la plus proche de ce que vous voulez faire, c'est Mesa. Plus bas niveau encore : Gallium.

C'est une implémentation, libre et open source d'OpenGL. Par contre, lorsqu'ils arrivent à jouer avec la carte graphique, c'est qu'ils ont compris comment elle fonctionnait, souvent en reverse engeenering.
24/05/2015, 09h49
Christophe

Citation:

C'est une implémentation, libre et open source d'OpenGL. Par contre, lorsqu'ils arrivent à jouer avec la carte graphique, c'est qu'ils ont compris comment elle fonctionnait, souvent en reverse engeenering.

Je rajouterai que du coup si ça marche pour une carte, ça ne marchera pas pour une autre.

J'ai tenté ce bout de code :

Code:

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
 
#include <utility>
#include <CL/cl.hpp>
#include <cstdio>
#include <cstdlib>
#include <fstream>
#include <iostream>
#include <string>
#include <iterator>
inline void checkErr(cl_int err, const char * name) {
    if (err != CL_SUCCESS) {
      std::cerr << "ERROR: " << name  << " (" << err << ")" << std::endl;
      exit(EXIT_FAILURE);
   }
}
const std::string hw("Hello World\n");
int main(void) {
    cl_int err;
    std::vector< cl::Platform > platformList;
    cl::Platform::get(&platformList);
    checkErr(platformList.size()!=0 ? CL_SUCCESS : -1, "cl::Platform::get");
    std::cerr << "Platform number is: " << platformList.size() << std::endl;std::string platformVendor;
    platformList[0].getInfo((cl_platform_info)CL_PLATFORM_VENDOR, &platformVendor);
    std::cerr << "Platform is by: " << platformVendor << "\n";
    cl_context_properties cprops[3] = {CL_CONTEXT_PLATFORM, (cl_context_properties)(platformList[0])(), 0};cl::Context context(
      CL_DEVICE_TYPE_GPU,
      cprops,
      NULL,
      NULL,
      &err);
    checkErr(err, "Context::Context()");
    return EXIT_SUCCESS;
}

Mais ça ne fonctionne pas, il me dit que je n'ai qu'une plateforme de type CPU, hors que j'ai bien une carte graphique dans mon ordinateur.

Je vais aller voir sur le forum d'openCL, si je ne peux pas trouver une solution à ce problème.

Car avec mesa ça fonctionne bien.

24/05/2015, 10h09
LittleWhite

Peut être vous avez deux entrées, dans platformList
24/05/2015, 13h21
Invité

Deux entrées dans une liste ? Je ne comprends pas bien...

En tout cas il n'y a qu'une plateforme dans la liste, remplacer le "0" par le "1" entre les corchets me donne une belle erreur de segmentation.

PS : la plateforme Intel permet d'utiliser les deux (CPU et GPU), maintenant, il ne me reste plus qu'à savoir comment utiliser l'un ou l'autre au niveau de l'api!

J'espère que ça ira mieux au niveau des perfs et je n'aurai sans doute plus ce problème de support du langage GLSL sur différentes carte graphiques!
24/05/2015, 14h15
mintho carmo

(sauf erreur de ma part, je crois que le but n'est pas de créer un driver GPU, mais de recréer le pipeline graphique en utilisant OpenCL. Pas pareil)

Niveau performance, cela m'étonnerait. OpenGL est assez bien supporté de nos jours, OpenCL probablement moins, et tu ne pourras implémenter que 1% (et c'est déjà beaucoup) des fonctionnalités d'OpenGL.

Mais si c'est juste pour le fun, ce n'est pas très grave de ne pas avoir un maximum de performances, suffit de continuer à utiliser OpenGL pour les "vrais" projets.

Lorsque tu as plusieurs device, le choix se fait lors de la création du contexte. Ensuite, tous les appels de fonction sur le contexte concerneront le device sélectionné.

Si tu ne vois qu'un seul device, c'est probablement que tu n'as pas le drivers OpenCL installés sont ton ordi.
25/05/2015, 21h49
Invité

J'ai juste besoin de 1% des fonctionnalités de openGL. ^^

La seule chose que je recherche maintenant c'est la performance..., je veux surtout voir si mon processeur intel sera capable d'appeler le bon device, pour le moment je n'ai qu'un device avec openCL, le CPU, mais j'ai peut être loupé quelque chose dans les tutoriels, il faut que je pose ma question sur le forum d'AMD.
25/05/2015, 22h13
mintho carmo

As tu installé les drivers de ta carte graphique AMD ? Et quels drivers ?

Citation:

As tu installé les drivers de ta carte graphique AMD ? Et quels drivers ?

-Le driver OpenCL.
-J'ai aussi installé mesa.

PS : J'ai modifier le code pour récupérer le second device d'id 1 mais ici j'ai une autre erreur de code en créant le contexte. (-30)
Code:

1 2 3 4 5 6 7 cl_context_properties cprops[3] = {CL_CONTEXT_PLATFORM, (cl_context_properties)(platformList[0])(), 1};cl::Context context( CL_DEVICE_TYPE_GPU, cprops, NULL, NULL, &err);
Comment est ce que je peux retrouvé l'erreur correspondant au code -30 ?

PS 2 : J'ai des valeurs invalide mais que dois je mettre comme valeurs si je veux utiliser le GPU ?

26/05/2015, 09h07
LittleWhite

Citation:

Envoyé par Lolilolight

PS 2 : J'ai des valeurs invalide mais que dois je mettre comme valeurs si je veux utiliser le GPU ?

En comparant avec les enums indiqués en bas de cette page : https://www.khronos.org/registry/cl/...ocs/man/xhtml/
Comme en OpenGL, j'ai envie de dire :).

Citation:

Envoyé par Lolilolight

PS : J'ai modifier le code pour récupérer le second device d'id 1 mais ici j'ai une autre erreur de code en créant le contexte. (-30)

Citation:

properties

Specifies a list of context property names and their corresponding values. Each property name is immediately followed by the corresponding desired value. The list is terminated with 0. properties can be NULL in which case the platform that is selected is implementation-defined. The list of supported properties is described in the table below.

Ce 0 n'est pas le numéro du device à-priori.

Cf doc wrapper C++, et doc openCL.

Tu as essayé un simple ?
Code:

1 2 3 4 5 6 7 8 9 10 11 12 13 14 15 cl_int err; cl::Context context(CL_DEVICE_TYPE_GPU, nullptr, nullptr, nullptr, &err); switch(err) { case CL_INVALID_PLATFORM: std::cout << "if properties is NULL and no platform could be selected or if platform value specified in properties is not a valid platform."; break; case CL_INVALID_VALUE: std::cout << "if context property name in properties is not a supported property name, or if pfn_notify is NULL but user_data is not NULL."; break; case CL_INVALID_VALUE: std::cout << "if pfn_notify is NULL but user_data is not NULL."; break; case CL_DEVICE_NOT_AVAILABLE: std::cout << "if no devices that match device_type are currently available."; break; case CL_DEVICE_NOT_FOUND: std::cout << " if no devices that match device_type were found."; break; case CL_OUT_OF_HOST_MEMORY: std::cout << " if there is a failure to allocate resources required by the OpenCL implementation on the host."; break; case CL_INVALID_DEVICE_TYPE: std::cout << " if device_type is not a valid value."; break; default: std::cout << "ok"; } std::cout << std::endl;

Oui mais ne fonctionne pas non plus. (J'ai le code d'erreur -1 à la création du contexte)

Mais j'ai une autre erreur aussi maintenant, en fait je voudrais rendre une face comportant n sommets (chaque faces comportant le même nombre de sommet est une instance), chaque instance peut avoir une matrice de transformation différente.

J'ai donc pensé à faire quelque chose comme ceci : (En ayant regroupé tout mes sommets utilisant le même matériel et appartenant au même type de face)

Je souhaiterais faire de l'indirect rendering, j'ai donc écrit le code suivant.

Code:

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
 
for (unsigned int i = 0; i < m_instances.size(); i++) {
                std::vector<float> transformMatrices;
                for (unsigned int j = 0; j < m_instances[i]->getTransforms().size(); j++) {
                    float* tmatrix = m_instances[i]->getTransforms()[j].get().getGlMatrix();
                    for (unsigned int n = 0; n < 16; n++) {
                        transformMatrices.push_back(tmatrix[n]);
                    }
                }
                cl_int err;
                ctransfMatrixBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, transformMatrices.size(), &transformMatrices, &err);
                checkErr(err, "Buffer::Buffer()");
                math::Matrix4f texM = (m_instances[i]->getMaterial().getTexture() != nullptr) ?
                    m_instances[i]->getMaterial().getTexture()->getTextureMatrix() :
                    math::Matrix4f();
                std::vector<float> vPosX = m_instances[i]->getVertexArray().m_vPosX;
                std::vector<float> vPosY = m_instances[i]->getVertexArray().m_vPosY;
                std::vector<float> vPosZ = m_instances[i]->getVertexArray().m_vPosZ;
                std::vector<float> vPosW = m_instances[i]->getVertexArray().m_vPosW;
                std::vector<unsigned char> vcRed = m_instances[i]->getVertexArray().m_vcRed;
                std::vector<unsigned char> vcBlue = m_instances[i]->getVertexArray().m_vcBlue;
                std::vector<unsigned char> vcGreen = m_instances[i]->getVertexArray().m_vcGreen;
                std::vector<unsigned char> vcAlpha = m_instances[i]->getVertexArray().m_vcAlpha;
                std::vector<unsigned int> ctx = m_instances[i]->getVertexArray().m_ctX;
                std::vector<unsigned int> cty = m_instances[i]->getVertexArray().m_ctY;
                std::vector<unsigned int> indexes = m_instances[i]->getVertexArray().m_indexes;
                std::vector<unsigned int> numIndexes = m_instances[i]->getVertexArray().m_numIndexes;
                std::vector<unsigned int> baseIndexes = m_instances[i]->getVertexArray().m_baseIndexes;
                std::vector<unsigned int> baseVertices = m_instances[i]->getVertexArray().m_baseVertices;
                unsigned int nbVerticesPerFaces = m_instances[i]->getVertexArray().nbVerticesPerFace;
                cvposXBuffer = cl::Buffer(clcontext, CL_MEM_READ_WRITE | CL_MEM_USE_HOST_PTR, vPosX.size(), &vPosX, &err);
                checkErr(err, "Buffer::Buffer()");
                cvposYBuffer = cl::Buffer(clcontext, CL_MEM_READ_WRITE | CL_MEM_USE_HOST_PTR, vPosX.size(), &vPosY, &err);
                checkErr(err, "Buffer::Buffer()");
                cvposZBuffer = cl::Buffer(clcontext, CL_MEM_READ_WRITE | CL_MEM_USE_HOST_PTR, vPosX.size(), &vPosZ, &err);
                checkErr(err, "Buffer::Buffer()");
                cvposWBuffer = cl::Buffer(clcontext, CL_MEM_READ_WRITE | CL_MEM_USE_HOST_PTR, vPosX.size(), &vPosW, &err);
                checkErr(err, "Buffer::Buffer()");
                cvcolredBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, vcRed.size(), &vcRed, &err);
                checkErr(err, "Buffer::Buffer()");
                cvcolgreenBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, vcBlue.size(), &vcBlue, &err);
                checkErr(err, "Buffer::Buffer()");
                cvcolblueBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, vcGreen.size(), &vcGreen, &err);
                checkErr(err, "Buffer::Buffer()");
                cvcolalphaBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, vcAlpha.size(), &vcAlpha, &err);
                checkErr(err, "Buffer::Buffer()");
                cvtexcoorduBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, ctx.size(), &ctx, &err);
                checkErr(err, "Buffer::Buffer()");
                cvtexcoordvBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, cty.size(), &cty, &err);
                checkErr(err, "Buffer::Buffer()");
                cvindexesBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, indexes.size(), &indexes, &err);
                checkErr(err, "Buffer::Buffer()");
                cnumIndexesBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, numIndexes.size(), &numIndexes, &err);
                checkErr(err, "Buffer::Buffer()");
                cbaseIndexesBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, baseIndexes.size(), &baseIndexes, &err);
                checkErr(err, "Buffer::Buffer()");
                cbaseVerticesBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, baseVertices.size(), &baseVertices, &err);
                checkErr(err, "Buffer::Buffer()");
                cNbVerticesPerFaces = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, 1, nbVerticesPerFaces, &err);
                checkErr(err, "Buffer::Buffer()");
                View& view = window.getView();
                ViewportMatrix vpm;
                vpm.setViewport(math::Vec3f(view.getViewport().getPosition().x, view.getViewport().getPosition().y, 0),
                math::Vec3f(view.getViewport().getWidth(), view.getViewport().getHeight(), 1));
                float* projMatrix = view.getProjMatrix().getMatrix().toGlMatrix();
                float* viewMatrix = view.getViewMatrix().getMatrix().toGlMatrix();
                float* viewportMatrix = vpm.getMatrix().toGlMatrix();
                cprojMatrixBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, 16, *projMatrix, &err);
                checkErr(err, "Buffer::Buffer()");
                cviewMatrixBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, 16, *viewMatrix, &err);
                checkErr(err, "Buffer::Buffer()");
                cvpMatrixBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, 16, *viewportMatrix, &err);
                std::vector<float> transfMatrices;
                checkErr(err, "Buffer::Buffer()");
                checkErr(err, "Buffer::Buffer()");
                err = clkvertexShader.setArg(0, cvposXBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(1, cvposYBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(2, cvposZBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(3, cvposWBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(4, cvcolredBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(5, cvcolblueBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(6, cvcolgreenBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(7, cvcolalphaBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(8, cvtexcoorduBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(9, cvtexcoordvBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(10, cvindexesBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(11, cnumIndexesBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(12, cbaseIndexesBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(13, cbaseVerticesBuffer);
                checkErr(err, "Kernel::setArg()");
                err = clkvertexShader.setArg(14, cNbVerticesPerFaces);
                checkErr(err, "Kernel::setArg()");
                cl::CommandQueue clqueue (clcontext, devices[0], 0, &err);
                checkErr(err, "CommandQueue::CommandQueue()");
                cl::Event event;
                err = clqueue.enqueueNDRangeKernel(clkvertexShader,
                                                    cl::NullRange, cl::NDRange(baseVertices.size() * nbVerticesPerFaces),
                                                    cl::NDRange(1, 1), NULL, &event);

Par exemple 1 point par face = des points, 2 = des lignes, 3 = des triangles, 4 = des quads, etc..., etc...
Et je n'aurai plus qu'à rasteriser.

Le soucis c'est que j'ai une erreur en compilation, je ne comprend pas car je n'avais pas ce problème de compilation au départ :

Code:

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
 
||=== Build: Release in ODFAEG (compiler: GNU GCC Compiler) ===|
||WARNING: Can't read file's timestamp: /home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Audio/ALCheck.cpp|
||WARNING: Can't read file's timestamp: /home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Audio/AudioDevice.cpp|
||warning: optimization flag '-fexpensive-optimizations' is not supported|
||warning: argument unused during compilation: '-fexpensive-optimizations'|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Math/../../../include/odfaeg/Core/fastDelegate.h|170|warning: 'RefVal' defined as a struct template here but previously declared as a class template [-Wmismatched-tags]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Math/../../../include/odfaeg/Core/fastDelegate.h|70|note: did you mean struct here?|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Math/../../../include/odfaeg/Core/resourceManager.h|528|warning: unused variable 'id' [-Wunused-variable]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/boundingVolume.h|60|warning: 'odfaeg::physic::BoundingVolume::intersects' hides overloaded virtual functions [-Woverloaded-virtual]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/boundingVolume.h|36|note: hidden overloaded virtual function 'odfaeg::physic::BaseInterface::intersects' declared here: type mismatch at 1st parameter ('odfaeg::physic::BoundingBox &' vs 'odfaeg::physic::BaseInterface &')|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/boundingVolume.h|37|note: hidden overloaded virtual function 'odfaeg::physic::BaseInterface::intersects' declared here: type mismatch at 1st parameter ('odfaeg::physic::BoundingSphere &' vs 'odfaeg::physic::BaseInterface &')|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/boundingVolume.h|38|note: hidden overloaded virtual function 'odfaeg::physic::BaseInterface::intersects' declared here: type mismatch at 1st parameter ('odfaeg::physic::BoundingEllipsoid &' vs 'odfaeg::physic::BaseInterface &')|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/boundingVolume.h|39|note: hidden overloaded virtual function 'odfaeg::physic::BaseInterface::intersects' declared here: type mismatch at 1st parameter ('odfaeg::physic::OrientedBoundingBox &' vs 'odfaeg::physic::BaseInterface &')|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/boundingVolume.h|40|note: hidden overloaded virtual function 'odfaeg::physic::BaseInterface::intersects' declared here: type mismatch at 1st parameter ('odfaeg::physic::BoundingPolyhedron &' vs 'odfaeg::physic::BaseInterface &')|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|187|warning: '&&' within '||' [-Wlogical-op-parentheses]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|187|note: place parentheses around the '&&' expression to silence this warning|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|187|warning: '&&' within '||' [-Wlogical-op-parentheses]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|187|note: place parentheses around the '&&' expression to silence this warning|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|292|warning: '&&' within '||' [-Wlogical-op-parentheses]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|292|note: place parentheses around the '&&' expression to silence this warning|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|292|warning: '&&' within '||' [-Wlogical-op-parentheses]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|292|note: place parentheses around the '&&' expression to silence this warning|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|416|warning: '&&' within '||' [-Wlogical-op-parentheses]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|416|note: place parentheses around the '&&' expression to silence this warning|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|416|warning: '&&' within '||' [-Wlogical-op-parentheses]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Physics/../Math/computer.h|416|note: place parentheses around the '&&' expression to silence this warning|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/../../../include/odfaeg/Graphics/../Math/../../../include/odfaeg/Core/stateParameter.h|32|warning: field 'name' will be initialized after field 'value' [-Wreorder]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp|254|warning: address of 'err' will always evaluate to 'true' [-Wpointer-bool-conversion]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp|263|warning: address of 'err' will always evaluate to 'true' [-Wpointer-bool-conversion]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp|265|warning: address of 'err' will always evaluate to 'true' [-Wpointer-bool-conversion]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp|267|warning: address of 'err' will always evaluate to 'true' [-Wpointer-bool-conversion]|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp|208|warning: unused variable 'texM' [-Wunused-variable]|
../../../../../usr/include/CL/cl.hpp|6175|error: no type named 'value_type' in 'std::iterator_traits<int>'|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp:254:39: note||in instantiation of function template specialization 'cl::Buffer::Buffer<int>' requested here|
../../../../../usr/include/CL/cl.hpp|6192|error: indirection requires pointer operand ('int' invalid)|
../../../../../usr/include/CL/cl.hpp|6373|error: no type named 'value_type' in 'std::iterator_traits<int>'|
../../../../../usr/include/CL/cl.hpp:6209:21: note||in instantiation of function template specialization 'cl::copy<int>' requested here|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp:254:39: note||in instantiation of function template specialization 'cl::Buffer::Buffer<int>' requested here|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h|387|error: no type named 'value_type' in 'std::iterator_traits<int>'|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h:432:23: note||in instantiation of function template specialization 'std::__copy_move_a<false, int, int *>' requested here|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h:464:20: note||in instantiation of function template specialization 'std::__copy_move_a2<false, int, int *>' requested here|
../../../../../usr/include/CL/cl.hpp:6392:10: note||in instantiation of function template specialization 'std::copy<int, int *>' requested here|
../../../../../usr/include/CL/cl.hpp:6209:21: note||in instantiation of function template specialization 'cl::copy<int>' requested here|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp:254:39: note||in instantiation of function template specialization 'cl::Buffer::Buffer<int>' requested here|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h|389|error: no type named 'iterator_category' in 'std::iterator_traits<int>'|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h|306|error: indirection requires pointer operand ('int' invalid)|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h:396:36: note||in instantiation of function template specialization 'std::__copy_move<false, false, int>::__copy_m<int, int *>' requested here|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h:432:23: note||in instantiation of function template specialization 'std::__copy_move_a<false, int, int *>' requested here|
/usr/bin/../lib/gcc/x86_64-linux-gnu/4.9/../../../../include/c++/4.9/bits/stl_algobase.h:464:20: note||in instantiation of function template specialization 'std::__copy_move_a2<false, int, int *>' requested here|
../../../../../usr/include/CL/cl.hpp:6392:10: note||in instantiation of function template specialization 'std::copy<int, int *>' requested here|
../../../../../usr/include/CL/cl.hpp:6209:21: note||in instantiation of function template specialization 'cl::copy<int>' requested here|
/home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp:254:39: note||in instantiation of function template specialization 'cl::Buffer::Buffer<int>' requested here|
||=== Build failed: 6 error(s), 33 warning(s) (0 minute(s), 2 second(s)) ===|

Voilà merci d'avance pour votre aide.

28/05/2015, 09h55
mintho carmo

Les warnings ne sont pas optionnels, il faut les corriger. Utilise -Werror

Quand tu donnes un fragment de code et les messages d'erreur correspondant, les numéros de ligne ne correspondent pas. Il faut dire a quelle ligne correspond les erreurs.

Je suppose que cela vient de cette ligne (et des suivantes ou tu utilises un cl::Buffer) :

Code:

ctransfMatrixBuffer = cl::Buffer(clcontext, CL_MEM_READ_ONLY | CL_MEM_USE_HOST_PTR, transformMatrices.size(), &transformMatrices, &err);

A quoi correspond ton &transformMatrices ? A priori, ce n'est pas bon
28/05/2015, 10h03
Invité

Citation:

A quoi correspond ton &transformMatrices ? A priori, ce n'est pas bon

Ca correspond à un vecteur de nombres flottants.

Chaque nombre est juste l'élément d'une matrice, je devrai surement utiliser un kernel à part pour effectuer les multiplications matricielles.
28/05/2015, 10h06
Iradrille
Citation:
Envoyé par Lolilolight

Code:

1 2 std::vector<float> vPosX = m_instances[i]->getVertexArray().m_vPosX; cvposXBuffer = cl::Buffer(clcontext, CL_MEM_READ_WRITE | CL_MEM_USE_HOST_PTR, vPosX.size(), &vPosX, &err);
Çà me semble suspect : il faut donner l'adresse des données, et non l'adresse du vector (?)

Code:

cvposXBuffer = cl::Buffer(clcontext, CL_MEM_READ_WRITE | CL_MEM_USE_HOST_PTR, vPosX.size(), vPosX.data(), &err);

Sinon, si je comprend bien tu n'entrelaces pas les données (c'est généralement conseillé), mais pire, tu fournis tes positions sous formes de 4 buffers différents, tu devrais vraiment regarder du coté de vec4.

edit : c'est aussi une copie possiblement inutile du vector, une ref constante serait probablement suffisante.

Justement je ne connais pas les différents types que je peux passer comme argument au kernel.

C'est pour ça que j'ai fait des std::vector sur des types primitifs. (float, unsigned char, unsigned int, etc...)

Ok donc c'est .data() que je dois utiliser pour avoir l'adresse du premier élément du vector.

Avec .data() ça compile bien avec les tableaux statiques (std::array) et dynamiques (std::vector), cependant, j'ai une dernière erreur ici :

La taille du buffer c'est le nombre de faces de même type multiplié par le nombre de sommets par faces, je peux alors, à l'aide des indices, récupérer tout les attributs de sommets et les matrices pour chaque instance indirectement.

Malheureusement, je ne parviens pas à passer la taille des buffers au kernel.
Code:

1 2 3 4 err = clqueue.enqueueNDRangeKernel(clkvertexShader, cl::NullRange, cl::NDRange(baseVertices.size() * nbVerticesPerFaces), cl::NDRange(1, 1), NULL, &event);
Ceci me génère une erreur de compilation :
Code:

1 2 /home/laurent/Développement/Projets-c++/ODFAEG/src/odfaeg/Graphics/cpuRenderComponent.cpp|304|error: invalid operands to binary expression ('size_type' (aka 'unsigned long') and 'std::vector<unsigned int>')|

28/05/2015, 12h51
mintho carmo

Le message d'erreur n'est pas complet.
A quoi correspond "std::vector<unsigned int>" dans la ligne de code que tu donnes ?
28/05/2015, 13h06
Invité

Citation:

Le message d'erreur n'est pas complet.
A quoi correspond "std::vector<unsigned int>" dans la ligne de code que tu donnes ?

A un vecteur d'unsigned int, en fait, ce sont toutes les positions des premiers sommet pour chaque face.

PS : je viens seulement de comprendre en fait il faut une constante, une carte graphique possède combien de mémoire cache en général ? (En gros, je peux stocker combien de vertex à la fois ?)
28/05/2015, 13h27
mintho carmo

Citation:

Envoyé par Lolilolight

A un vecteur d'unsigned int, en fait, ce sont toutes les positions des premiers sommet pour chaque face.

Merci... On recommence.
A quelle variable correspond ce type ? Dans la ligne de code que tu donnes, tu utilises baseVertices.size() (le size_type probablement du message d'erreur) et nbVerticesPerFaces (un unsigned int). Donc d'ou vient le "std::vector<unsigned int>" donné dans le message d'erreur ?
(dit autrement, le message d'erreur ne semble pas correspondre a la ligne de code que tu donnes)

Citation:

Envoyé par Lolilolight

PS : je viens seulement de comprendre en fait il faut une constante, une carte graphique possède combien de mémoire cache en général ? (En gros, je peux stocker combien de vertex à la fois ?)

Tu confonds (encore) mémoire cache et mémoire du GPU. La première : quelques ko, la seconde en général au moins 1 Go (sauf probablement sur embarqué).
28/05/2015, 13h28
mintho carmo

Et qu'est ce qui doit etre constant ???

Citation:

Et qu'est ce qui doit etre constant ???

Ca ne compilait pas car le troisième paramètre de cette fonction devait être un litéral constant :

Code:

1
2
3
4
 
err = clqueue.enqueueNDRangeKernel(clkvertexShader,
                                                    cl::NullRange, <s>cl::NDRange(baseVertices.size() * nbVerticesPerFaces</s> 1024),
                                                    cl::NDRange(1, 1), NULL, &event);

Mais que fait cette fonction exactement, je ne suis pas sûr de bien la comprendre, la seule chose que j'ai compris est qu'elle réserve un espace mémoire (workgroup) utilisé par tout les threads, et chaque thread utilise un espace mémoire appelé work-item, et ça fait ainsi comme une sorte de tableau, mais, comment parcourir ce tableau afin de récupérer les bons ids ?

Par exemple cl::NDRange me génère un thread id par appel au kernel que je récupère avec get_global_id, NDRange(0, 4) va me générer deux thread id qui vont de 0 à 4 alors ?

Au sinon voici le code que j'ai pour le moment, qui utilise un thread par vertex, mais, je ne sais pas si je le laisse ainsi ou si j'utilise un thread par face plutôt, ça, ça dépendra beaucoup des performances de ma machine.

Voici le code que j'ai en ce moment :

Code:

1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
 
#pragma OPENCL EXTENSION cl_khr_byte_addressable_store : enable
//Multiply two 4*4 matrices.
float16 multMat (float16 matA, float16 matB) {
    float16 matC;        
    for (int x = 0; x < 4; ++x) {
	for (int y = 0; y < 4; ++y) {
            float value = 0;
	    for (int k = 0; k < 4; ++k) {
		float elementA = matA[y * 4 + k];
                float elementB = matB[k * 4 + x];
		value += elementA * elementB;
	    }
	    matC[y * 4 + x] = value;		
        }
    }
    return matC;
}
//Multiply a 4*4 matrix with a vec4.
float4 multVec (float16 matA, float4 vecB) {
   float4 vecC;
   for (int i = 0; i < 4; ++i) {
        float value = 0;
	for (int j = 0; j < 4; ++j) {
             value += vecB[j] * matA[i][j];
	}
	vecC[i] = value;
   }
   return vecC;
}
//Transpose a 4*4 matrix.
float16 transpose(float16 matA) {
	float16 matT
	for (int i = 0; i < 4; ++i) {        	
		for (int j = 0; j < 4; ++j) {
			matT[i][j] = matA[j][i];
		}
	}
	return matT;
}
//Convert vertex position from object space toviewport space.
__kernel void vertexShader(__global float* vPosX, __global float* vPosY, __global float* vPosZ, __global float* vPosW,
                           __global unsigned int* vColRed, __global unsigned int* vColBlue, __global unsigned int* vColGreen, 				   __global unsigned int* vColAlpha, __global int* vTCU, __global int* vTCV, 
			   __global unsigned int* indices,  __global unsigned int numIndices, __global unsigned int* baseIndices, 
			   __global unsigned int* baseVertices,  __global unsigned int* nbVerticesPerFaces, __global float* transfMatrices, 				   __global float16 projMatrix, __global float16 viewMatrix, __global float16 viewportMatrix, 
			   __global int nbVertices) {
        size_t tid = get_global_id(0);
	if (tid < nbVertices) {		
		int instanceID = tid / nbVerticesPerFace;
		float16 transfMatrix;
		float4 position = (float4) (vPosX[indices[tid]], vPosY[indices[tid]], vPosZ[indices[tid]], vPosW[indices[tid]]);
		for (int i = 0; i < 16; i++) {
		    transfMatrix[i] = transfMatrices[instanceID*16+i];
		}					
		float4 worldcoords = multVec(transfMatrix, position);
		float4 viewcoords = multVec(viewMatrix, worldcoords);
                float4 clipcoords = multVec(projMatrix, viewcoords);
		float4 ndcCoords = clipcoords / clipcoords.w;
		position = multVec(viewportMatrix, ndcCoords);
		vPosX[tid] = abs(position.x);
                vPosY[tid] = abs(position.y);
                vPosZ[tid] = abs(position.z);
                vPosW[tid] = position.w; 
	}
 
}

30/05/2015, 13h06
mintho carmo

Citation:

Envoyé par Lolilolight

Ca ne compilait pas car le troisième paramètre de cette fonction devait être un litéral constant

Le 3ème paramètre est juste un cl_uint passé par valeur. Tu n'es pas obligé de passer une littérale (heureusement).
(cours de C++ débutant)

Citation:

Envoyé par Lolilolight

Mais que fait cette fonction exactement, je ne suis pas sûr de bien la comprendre, la seule chose que j'ai compris est qu'elle réserve un espace mémoire (workgroup) utilisé par tout les threads, et chaque thread utilise un espace mémoire appelé work-item, et ça fait ainsi comme une sorte de tableau, mais, comment parcourir ce tableau afin de récupérer les bons ids ?

Par exemple cl::NDRange me génère un thread id par appel au kernel que je récupère avec get_global_id, NDRange(0, 4) va me générer deux thread id qui vont de 0 à 4 alors ?

Ouch.
Tu utilises quel cours ou livre pour étudier OpenCL ?
Tu mélanges complètement les concepts, n'utilises pas correctement les termes techniques.
Tu vas faire n'importe quoi si tu n'étudies pas sérieusement les choses.

Citation:

Envoyé par Lolilolight

Au sinon voici le code que j'ai pour le moment, qui utilise un thread par vertex, mais, je ne sais pas si je le laisse ainsi ou si j'utilise un thread par face plutôt, ça, ça dépendra beaucoup des performances de ma machine.

L'équivalent OpenGL dépend du stage dans le pipeline :
- un thread par géométrie dans les geometry shader et tesselation shader
- un thread par vertex dans le vertex shader
- un thread pas pixel dans le fragment/pixel shader
Donc tout dépend de ce que tu veux faire
30/05/2015, 13h43
Iradrille

Citation:

Envoyé par mintho carmo

- un thread pas pixel dans le fragment/pixel shader

Je croyais que c'était un thread par fragment, avec un fragment = 4 (valeur fixe ? dépendante du matériel ?) pixels ?
30/05/2015, 14h05
LittleWhite

Oui Iradrille, c'est un thread par fragment (d'ailleurs on devrait dire fragment shader) et le nombre de pixel géré par fragment dépend du matériel.
Mais bon, on peux résumer/extrapoler en disant un thread par pixel, car au final, nous voyons (dans le pixel shader/thread) que le pixel (et non le fragment) et c'est la carte graphique qui split le fragment, si jamais il y a deux pixels n'ayant pas les mêmes couleurs (genre, sur les bordures de mesh).
30/05/2015, 14h41
Invité

Ou se trouvent les messages d'erreur de compilation pour les fichiers .cl ?

PS : Il me faudrait un bouquin ou quelque chose du genre sur openCL car là, ça devient compliqué. :/