Skip to content

Commit 811af03

Browse files
memomemo
committed
first commit
0 parents  commit 811af03

29 files changed

+3351
-0
lines changed

‎.gitignore

+85
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,85 @@
1+
# Some general ignore patterns
2+
3+
*/bin/*
4+
!*/bin/data/
5+
# for bin folder in root
6+
/bin/*
7+
!/bin/data/
8+
9+
build/
10+
obj/
11+
*.o
12+
Debug*/
13+
Release*/
14+
*.mode*
15+
*.app/
16+
*.pyc
17+
.svn/
18+
19+
# IDE-specific ignore patterns (e.g. user-specific files)
20+
21+
#XCode
22+
*.pbxuser
23+
*.perspective
24+
*.perspectivev3
25+
*.mode1v3
26+
*.mode2v3
27+
#XCode 4
28+
xcuserdata
29+
*.xcworkspace
30+
31+
#Code::Blocks
32+
*.depend
33+
*.layout
34+
*.cbTemp
35+
36+
#Visual Studio
37+
*.sdf
38+
*.opensdf
39+
*.suo
40+
ipch/
41+
42+
#Eclipse
43+
.metadata
44+
local.properties
45+
.externalToolBuilders
46+
47+
# OS-specific ignore patterns
48+
49+
#Linux
50+
*~
51+
# KDE
52+
.directory
53+
54+
#OSX
55+
.DS_Store
56+
*.swp
57+
*~.nib
58+
# Thumbnails
59+
._*
60+
61+
#Windows
62+
# Windows image file caches
63+
Thumbs.db
64+
# Folder config file
65+
Desktop.ini
66+
67+
#Android
68+
.csettings
69+
70+
# Packages
71+
# it's better to unpack these files and commit the raw source
72+
# git has its own built in compression methods
73+
*.7z
74+
*.dmg
75+
*.gz
76+
*.iso
77+
*.jar
78+
*.rar
79+
*.tar
80+
*.zip
81+
82+
# Logs and databases
83+
*.log
84+
*.sql
85+
*.sqlite

‎README.md

+61
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,61 @@
1+
ofxMSAOpenCL
2+
=====================================
3+
4+
Introduction
5+
------------
6+
C++ openFrameworks addon for very simple to use wrapper for OpenCL. All underlying openCL objects are accessible to allow advanced features too if need be.
7+
Demo (1M particles @ 100-200 fps) at [vimeo.com/7332496](http://vimeo.com/7332496)
8+
9+
Licence
10+
-------
11+
The code in this repository is available under the [MIT License](https://secure.wikimedia.org/wikipedia/en/wiki/Mit_license).
12+
Copyright (c) 2008-2012 Memo Akten, [www.memo.tv](http://www.memo.tv)
13+
The Mega Super Awesome Visuals Company
14+
15+
16+
Installation
17+
------------
18+
Copy to your openFrameworks/addons folder.
19+
20+
Dependencies
21+
------------
22+
none
23+
24+
Compatibility
25+
------------
26+
OF0072
27+
28+
29+
Known issues
30+
------------
31+
none
32+
33+
Version history
34+
------------
35+
### v2.1 23/09/2012
36+
- compatible with OF0072
37+
- renamed (uppercase) MSA namespace to (lowercase) msa. (kept MSA as an alias for backwards compatibility)
38+
- no longer requires MSACore
39+
40+
### v2.0
41+
- move to centralized MSALibs (requires MSACore)
42+
- everything is MSA:: namespace
43+
44+
### v0.3
45+
- added image support
46+
- restructured buffer/memory management
47+
- minor break in backwards compatability: createBuffer returns ofxOpenCLBuffer instead of cl_mem. so
48+
- writeBuffer and readBuffer are methods of ofxOpenCLBuffer, not ofxOpenCL
49+
- when passing buffer (or image) as parameter to ofxOpenCLKernel::setArg, use ofxOpenCLBuffer::getMemoryObject() (which returns the cl_mem)
50+
51+
### v0.2
52+
- added support for multiple devices
53+
- sharing context with opengl (only on mac osx at the moment)
54+
- better handling of multi-dimensional data (minor backwards compatability break with kernel::run)
55+
- support for opengl/opencl buffer+texture sharing
56+
- can load programs from binary (support for creating binary coming soon)
57+
58+
59+
### v0.1
60+
- initial version
61+

‎example-Hello World/data/MSAOpenCL/HelloWorld.cl

+18
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,18 @@
1+
//--------------------------------------------------------------
2+
__kernel void inverse(__global float *a, __global float *result) {
3+
int gid = get_global_id(0);
4+
result[gid] = 1.0f/a[gid];
5+
}
6+
7+
//--------------------------------------------------------------
8+
__kernel void square(__global float *a, __global float *result) {
9+
int gid = get_global_id(0);
10+
result[gid] = a[gid] * a[gid];
11+
}
12+
13+
//--------------------------------------------------------------
14+
__kernel void multiplyScaler(__global float *a, __global float b, __global float *result) {
15+
int gid = get_global_id(0);
16+
result[gid] = a[gid] * b;
17+
}
18+

‎example-Hello World/src/main.cpp

+16
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,16 @@
1+
#include "ofMain.h"
2+
#include "testApp.h"
3+
#include "ofAppGlutWindow.h"
4+
5+
//========================================================================
6+
int main( ){
7+
8+
ofAppGlutWindow window;
9+
ofSetupOpenGL(&window, 1024,768, OF_WINDOW); // <-------- setup the GL context
10+
11+
// this kicks off the running of my app
12+
// can be OF_WINDOW or OF_FULLSCREEN
13+
// pass in width and height too:
14+
ofRunApp( new testApp());
15+
16+
}

‎example-Hello World/src/testApp.cpp

+111
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,111 @@
1+
#include "testApp.h"
2+
3+
#include "MSAOpenCL.h"
4+
#include "MSATimer.h"
5+
6+
#define SIZE (2048*2048)
7+
#define REPS 500
8+
9+
msa::OpenCL openCL;
10+
float buf[2][SIZE];
11+
msa::OpenCLBuffer clBuf[2];
12+
float scalerMultipler;
13+
14+
float testBuffer[SIZE];
15+
16+
msa::Timer timer;
17+
18+
//--------------------------------------------------------------
19+
void testApp::setup(){
20+
21+
// dump everything to console
22+
ofSetLogLevel(OF_LOG_VERBOSE);
23+
24+
// initialize input data
25+
for(int i=0;i<SIZE; i++){
26+
buf[0][i] = i+1;
27+
}
28+
29+
30+
// setup openCL, load program and init kernels
31+
openCL.setup(CL_DEVICE_TYPE_GPU, 2);
32+
openCL.loadProgramFromFile("MSAOpenCL/HelloWorld.cl", false);
33+
msa::OpenCLKernel *kernelSquare = openCL.loadKernel("square");
34+
msa::OpenCLKernel *kernelInverse = openCL.loadKernel("inverse");
35+
msa::OpenCLKernel *kernelMultiplyScaler = openCL.loadKernel("multiplyScaler");
36+
37+
38+
// create openCL buffers and upload initial data
39+
printf("\nPlease wait while preparing buffers...");
40+
timer.start();
41+
clBuf[0].initBuffer(SIZE * sizeof(float), CL_MEM_READ_WRITE, buf[0]);
42+
clBuf[1].initBuffer(SIZE * sizeof(float), CL_MEM_READ_WRITE);
43+
44+
kernelSquare->setArg(0, clBuf[0].getCLMem());
45+
kernelSquare->setArg(1, clBuf[1].getCLMem());
46+
47+
kernelInverse->setArg(0, clBuf[1].getCLMem());
48+
kernelInverse->setArg(1, clBuf[0].getCLMem());
49+
50+
kernelMultiplyScaler->setArg(0, clBuf[0].getCLMem());
51+
kernelMultiplyScaler->setArg(1, scalerMultipler);
52+
kernelMultiplyScaler->setArg(2, clBuf[1].getCLMem());
53+
openCL.finish(); // not normally needed, but here for more precise time measurement
54+
55+
timer.stop();
56+
printf("took %f seconds\n", timer.getSeconds());
57+
58+
59+
60+
// run kernels
61+
printf("\nPlease wait while running kernels...");
62+
timer.start();
63+
size_t sizes[1] = { SIZE };
64+
for(int r=0; r<REPS; r++) {
65+
// run these kernels passing in a sizes array
66+
kernelSquare->run(1, sizes);
67+
kernelInverse->run(1, sizes);
68+
69+
// running this one with the run1D wrapper, just to show how it works
70+
// actualy it does the same as the above run method (except it internally creates the array everytime its run)
71+
kernelMultiplyScaler->run1D(SIZE);
72+
}
73+
openCL.finish(); // not normally needed, but here for more precise time measurement
74+
timer.stop();
75+
printf("took %f seconds\n", timer.getSeconds());
76+
77+
78+
79+
// read results back from openCL device
80+
printf("\nPlease wait while reading back buffer...");
81+
timer.start();
82+
clBuf[0].read(buf[1], 0, SIZE * sizeof(float));
83+
timer.stop();
84+
printf("took %f seconds\n", timer.getSeconds());
85+
86+
87+
88+
// perform operation on CPU as well to compare results
89+
printf("\nPlease wait while running on CPU for comparison...");
90+
timer.start();
91+
for(int r=0; r<REPS; r++) {
92+
for(int i=0; i<SIZE; i++) testBuffer[i] = (buf[0][i] * buf[0][i]);
93+
for(int i=0; i<SIZE; i++) testBuffer[i] = 1.0f/testBuffer[i];
94+
for(int i=0; i<SIZE; i++) testBuffer[i] = testBuffer[i] * scalerMultipler;
95+
}
96+
openCL.finish(); // not normally needed, but here for more precise time measurement
97+
timer.stop();
98+
printf("took %f seconds\n", timer.getSeconds());
99+
100+
101+
102+
// compare results
103+
float diffSum = 0;
104+
for(int i=0; i<SIZE; i++) {
105+
float diff = testBuffer[i] - buf[1][i];
106+
// printf("input:%f outputCL:%f outputTest:%f diff:%f\n", buf[0][i], buf[1][i], testBuffer[i], diff);
107+
}
108+
printf("\n\noutput diffSum: %f\n\n", diffSum);
109+
110+
std::exit(0);
111+
}

‎example-Hello World/src/testApp.h

+13
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,13 @@
1+
#ifndef _TEST_APP
2+
#define _TEST_APP
3+
4+
5+
#include "ofMain.h"
6+
7+
class testApp : public ofBaseApp {
8+
9+
public:
10+
void setup();
11+
};
12+
13+
#endif

0 commit comments

Comments
 (0)