bool ProcessingChainBase::set_plugin_list(const list<Plugin*> &p) {
if (lists_equal(p, modules, &next_commit_needs_ramp)) {
return false;
}
wait_latch();
if (check_release()) {
release();
}
typedef set<const char*, stringcomp> pchar_set;
pchar_set new_ids;
for (list<Plugin*>::const_iterator i = p.begin(); i != p.end(); ++i) {
new_ids.insert((*i)->get_pdef()->id);
}
for (list<Plugin*>::const_iterator i = modules.begin(); i != modules.end(); ++i) {
if (!(*i)->get_pdef()->activate_plugin) {
continue;
}
pchar_set::iterator r = new_ids.find((*i)->get_pdef()->id);
if (r == new_ids.end()) {
to_release.push_back(*i);
}
}
modules = p;
return true;
}
static void test_ID3DXSprite(IDirect3DDevice9 *device)
{
ID3DXSprite *sprite;
IDirect3D9 *d3d;
IDirect3DDevice9 *cmpdev;
IDirect3DTexture9 *tex1, *tex2;
D3DXMATRIX mat, cmpmat;
D3DVIEWPORT9 vp;
RECT rect;
D3DXVECTOR3 pos, center;
HRESULT hr;
IDirect3DDevice9_GetDirect3D(device, &d3d);
hr = IDirect3D9_CheckDeviceFormat(d3d, D3DADAPTER_DEFAULT, D3DDEVTYPE_HAL, D3DFMT_X8R8G8B8, D3DUSAGE_DYNAMIC, D3DRTYPE_TEXTURE, D3DFMT_A8R8G8B8);
IDirect3D9_Release(d3d);
ok (hr == D3D_OK, "D3DFMT_A8R8G8B8 not supported\n");
if (FAILED(hr)) return;
hr = IDirect3DDevice9_CreateTexture(device, 64, 64, 1, 0, D3DFMT_A8R8G8B8, D3DPOOL_DEFAULT, &tex1, NULL);
ok (hr == D3D_OK, "Failed to create first texture (error code: %#x)\n", hr);
if (FAILED(hr)) return;
hr = IDirect3DDevice9_CreateTexture(device, 32, 32, 1, 0, D3DFMT_A8R8G8B8, D3DPOOL_DEFAULT, &tex2, NULL);
ok (hr == D3D_OK, "Failed to create second texture (error code: %#x)\n", hr);
if (FAILED(hr)) {
IDirect3DTexture9_Release(tex1);
return;
}
/* Test D3DXCreateSprite */
hr = D3DXCreateSprite(device, NULL);
ok (hr == D3DERR_INVALIDCALL, "D3DXCreateSprite returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = D3DXCreateSprite(NULL, &sprite);
ok (hr == D3DERR_INVALIDCALL, "D3DXCreateSprite returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = D3DXCreateSprite(device, &sprite);
ok (hr == D3D_OK, "D3DXCreateSprite returned %#x, expected %#x\n", hr, D3D_OK);
/* Test ID3DXSprite_GetDevice */
hr = ID3DXSprite_GetDevice(sprite, NULL);
ok (hr == D3DERR_INVALIDCALL, "GetDevice returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = ID3DXSprite_GetDevice(sprite, &cmpdev); /* cmpdev == NULL */
ok (hr == D3D_OK, "GetDevice returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_GetDevice(sprite, &cmpdev); /* cmpdev != NULL */
ok (hr == D3D_OK, "GetDevice returned %#x, expected %#x\n", hr, D3D_OK);
IDirect3DDevice9_Release(device);
IDirect3DDevice9_Release(device);
/* Test ID3DXSprite_GetTransform */
hr = ID3DXSprite_GetTransform(sprite, NULL);
ok (hr == D3DERR_INVALIDCALL, "GetTransform returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = ID3DXSprite_GetTransform(sprite, &mat);
ok (hr == D3D_OK, "GetTransform returned %#x, expected %#x\n", hr, D3D_OK);
if(SUCCEEDED(hr)) {
D3DXMATRIX identity;
D3DXMatrixIdentity(&identity);
check_mat(mat, identity);
}
/* Test ID3DXSprite_SetTransform */
/* Set a transform and test if it gets returned correctly */
U(mat).m[0][0]=2.1f; U(mat).m[0][1]=6.5f; U(mat).m[0][2]=-9.6f; U(mat).m[0][3]=1.7f;
U(mat).m[1][0]=4.2f; U(mat).m[1][1]=-2.5f; U(mat).m[1][2]=2.1f; U(mat).m[1][3]=5.5f;
U(mat).m[2][0]=-2.6f; U(mat).m[2][1]=0.3f; U(mat).m[2][2]=8.6f; U(mat).m[2][3]=8.4f;
U(mat).m[3][0]=6.7f; U(mat).m[3][1]=-5.1f; U(mat).m[3][2]=6.1f; U(mat).m[3][3]=2.2f;
hr = ID3DXSprite_SetTransform(sprite, NULL);
ok (hr == D3DERR_INVALIDCALL, "SetTransform returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = ID3DXSprite_SetTransform(sprite, &mat);
ok (hr == D3D_OK, "SetTransform returned %#x, expected %#x\n", hr, D3D_OK);
if(SUCCEEDED(hr)) {
hr=ID3DXSprite_GetTransform(sprite, &cmpmat);
if(SUCCEEDED(hr)) check_mat(cmpmat, mat);
else skip("GetTransform returned %#x\n", hr);
}
/* Test ID3DXSprite_SetWorldViewLH/RH */
todo_wine {
hr = ID3DXSprite_SetWorldViewLH(sprite, &mat, &mat);
ok (hr == D3D_OK, "SetWorldViewLH returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_SetWorldViewLH(sprite, NULL, &mat);
ok (hr == D3D_OK, "SetWorldViewLH returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_SetWorldViewLH(sprite, &mat, NULL);
ok (hr == D3D_OK, "SetWorldViewLH returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_SetWorldViewLH(sprite, NULL, NULL);
ok (hr == D3D_OK, "SetWorldViewLH returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_SetWorldViewRH(sprite, &mat, &mat);
ok (hr == D3D_OK, "SetWorldViewRH returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_SetWorldViewRH(sprite, NULL, &mat);
ok (hr == D3D_OK, "SetWorldViewRH returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_SetWorldViewRH(sprite, &mat, NULL);
ok (hr == D3D_OK, "SetWorldViewRH returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_SetWorldViewRH(sprite, NULL, NULL);
ok (hr == D3D_OK, "SetWorldViewRH returned %#x, expected %#x\n", hr, D3D_OK);
}
IDirect3DDevice9_BeginScene(device);
/* Test ID3DXSprite_Begin*/
hr = ID3DXSprite_Begin(sprite, 0);
ok (hr == D3D_OK, "Begin returned %#x, expected %#x\n", hr, D3D_OK);
IDirect3DDevice9_GetTransform(device, D3DTS_WORLD, &mat);
D3DXMatrixIdentity(&cmpmat);
check_mat(mat, cmpmat);
IDirect3DDevice9_GetTransform(device, D3DTS_VIEW, &mat);
check_mat(mat, cmpmat);
IDirect3DDevice9_GetTransform(device, D3DTS_PROJECTION, &mat);
IDirect3DDevice9_GetViewport(device, &vp);
D3DXMatrixOrthoOffCenterLH(&cmpmat, vp.X+0.5f, (float)vp.Width+vp.X+0.5f, (float)vp.Height+vp.Y+0.5f, vp.Y+0.5f, vp.MinZ, vp.MaxZ);
check_mat(mat, cmpmat);
/* Test ID3DXSprite_Flush and ID3DXSprite_End */
hr = ID3DXSprite_Flush(sprite);
ok (hr == D3D_OK, "Flush returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_End(sprite);
ok (hr == D3D_OK, "End returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Flush(sprite); /* May not be called before next Begin */
ok (hr == D3DERR_INVALIDCALL, "Flush returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = ID3DXSprite_End(sprite);
ok (hr == D3DERR_INVALIDCALL, "End returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
/* Test ID3DXSprite_Draw */
hr = ID3DXSprite_Begin(sprite, 0);
ok (hr == D3D_OK, "Begin returned %#x, expected %#x\n", hr, D3D_OK);
if(FAILED(hr)) skip("Couldn't ID3DXSprite_Begin, can't test ID3DXSprite_Draw\n");
else { /* Feed the sprite batch */
int texref1, texref2;
SetRect(&rect, 53, 12, 142, 165);
pos.x = 2.2f; pos.y = 4.5f; pos.z = 5.1f;
center.x = 11.3f; center.y = 3.4f; center.z = 1.2f;
texref1 = get_ref((IUnknown*)tex1);
texref2 = get_ref((IUnknown*)tex2);
hr = ID3DXSprite_Draw(sprite, NULL, &rect, ¢er, &pos, D3DCOLOR_XRGB(255, 255, 255));
ok (hr == D3DERR_INVALIDCALL, "Draw returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = ID3DXSprite_Draw(sprite, tex1, &rect, ¢er, &pos, D3DCOLOR_XRGB(255, 255, 255));
ok (hr == D3D_OK, "Draw returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Draw(sprite, tex2, &rect, ¢er, &pos, D3DCOLOR_XRGB( 3, 45, 66));
ok (hr == D3D_OK, "Draw returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Draw(sprite, tex1, NULL, ¢er, &pos, D3DCOLOR_XRGB(255, 255, 255));
ok (hr == D3D_OK, "Draw returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Draw(sprite, tex1, &rect, NULL, &pos, D3DCOLOR_XRGB(255, 255, 255));
ok (hr == D3D_OK, "Draw returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Draw(sprite, tex1, &rect, ¢er, NULL, D3DCOLOR_XRGB(255, 255, 255));
ok (hr == D3D_OK, "Draw returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Draw(sprite, tex1, NULL, NULL, NULL, 0);
ok (hr == D3D_OK, "Draw returned %#x, expected %#x\n", hr, D3D_OK);
check_ref((IUnknown*)tex1, texref1+5); check_ref((IUnknown*)tex2, texref2+1);
hr = ID3DXSprite_Flush(sprite);
ok (hr == D3D_OK, "Flush returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Flush(sprite); /* Flushing twice should work */
ok (hr == D3D_OK, "Flush returned %#x, expected %#x\n", hr, D3D_OK);
check_ref((IUnknown*)tex1, texref1); check_ref((IUnknown*)tex2, texref2);
hr = ID3DXSprite_End(sprite);
ok (hr == D3D_OK, "End returned %#x, expected %#x\n", hr, D3D_OK);
}
/* Test ID3DXSprite_OnLostDevice and ID3DXSprite_OnResetDevice */
/* Both can be called twice */
hr = ID3DXSprite_OnLostDevice(sprite);
ok (hr == D3D_OK, "OnLostDevice returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_OnLostDevice(sprite);
ok (hr == D3D_OK, "OnLostDevice returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_OnResetDevice(sprite);
ok (hr == D3D_OK, "OnResetDevice returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_OnResetDevice(sprite);
ok (hr == D3D_OK, "OnResetDevice returned %#x, expected %#x\n", hr, D3D_OK);
/* Make sure everything works like before */
hr = ID3DXSprite_Begin(sprite, 0);
ok (hr == D3D_OK, "Begin returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Draw(sprite, tex2, &rect, ¢er, &pos, D3DCOLOR_XRGB(255, 255, 255));
ok (hr == D3D_OK, "Draw returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_Flush(sprite);
ok (hr == D3D_OK, "Flush returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_End(sprite);
ok (hr == D3D_OK, "End returned %#x, expected %#x\n", hr, D3D_OK);
/* OnResetDevice makes the interface "forget" the Begin call */
hr = ID3DXSprite_Begin(sprite, 0);
ok (hr == D3D_OK, "Begin returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_OnResetDevice(sprite);
ok (hr == D3D_OK, "OnResetDevice returned %#x, expected %#x\n", hr, D3D_OK);
hr = ID3DXSprite_End(sprite);
ok (hr == D3DERR_INVALIDCALL, "End returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
IDirect3DDevice9_EndScene(device);
check_release((IUnknown*)sprite, 0);
check_release((IUnknown*)tex2, 0);
check_release((IUnknown*)tex1, 0);
}
void test_resource_manager(void)
{
enum ia_css_err rval = 0;
uint32_t resource_id_q = 0;
uint32_t resource_id_thread = 0;
//sh_css_set_dtrace_level(9);
rval = ia_css_i_host_rmgr_init_gen(IA_CSS_RESOURCE_SP_THREAD);
assert(rval ==IA_CSS_SUCCESS);
rval = ia_css_i_host_rmgr_init_gen(IA_CSS_RESOURCE_HOST2SP_QUEUE);
assert(rval ==IA_CSS_SUCCESS);
rval = ia_css_i_host_rmgr_setup_gen(IA_CSS_RESOURCE_SP_THREAD, 10);
assert(rval ==IA_CSS_SUCCESS);
rval = ia_css_i_host_rmgr_setup_gen(IA_CSS_RESOURCE_HOST2SP_QUEUE, 1111);
assert(rval!= IA_CSS_SUCCESS);
rval = ia_css_i_host_rmgr_setup_gen(IA_CSS_RESOURCE_HOST2SP_QUEUE, 1);
assert(rval == IA_CSS_SUCCESS);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 0, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 1, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 2, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 3, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 4, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 5, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 6, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 7, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 8, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 9, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, IA_CSS_RESOURCE_LIST_MAX_AMOUNT, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, IA_CSS_RESOURCE_LIST_MAX_AMOUNT + 1, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, IA_CSS_RESOURCE_LIST_MAX_AMOUNT + 100, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 0, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 1, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 2, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 3, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 4, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 5, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 6, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 7, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 8, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 9, 1);
check_release(IA_CSS_RESOURCE_SP_THREAD, 3, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 8, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 2, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 7, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 7, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 2, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 3, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 7, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 8, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 8, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 0, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 1, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 2, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 3, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 4, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 5, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 6, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 7, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 8, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 9, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, IA_CSS_RESOURCE_LIST_MAX_AMOUNT, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, IA_CSS_RESOURCE_LIST_MAX_AMOUNT + 1, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, IA_CSS_RESOURCE_LIST_MAX_AMOUNT + 100, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 0, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 1, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 2, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 3, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 4, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 5, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 6, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 7, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 8, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 9, 1);
check_release(IA_CSS_RESOURCE_HOST2SP_QUEUE, 3, 0);
check_release(IA_CSS_RESOURCE_HOST2SP_QUEUE, 8, 0);
check_release(IA_CSS_RESOURCE_HOST2SP_QUEUE, 2, 0);
check_release(IA_CSS_RESOURCE_HOST2SP_QUEUE, 7, 0);
check_release(IA_CSS_RESOURCE_HOST2SP_QUEUE, 7, 1);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 2, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 3, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 7, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 8, 0);
check_aquire(IA_CSS_RESOURCE_HOST2SP_QUEUE, &resource_id_q, 8, 1);
check_release(IA_CSS_RESOURCE_SP_THREAD, 1, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 2, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 3, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 4, 0);
check_release(IA_CSS_RESOURCE_SP_THREAD, 2, 1);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 1, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 2, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 3, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 4, 0);
check_aquire(IA_CSS_RESOURCE_SP_THREAD, &resource_id_thread, 5, 1);
}
static void test_ID3DXFont(IDirect3DDevice9 *device)
{
D3DXFONT_DESC desc;
ID3DXFont *font;
HRESULT hr;
int ref;
/* D3DXCreateFont */
ref = get_ref((IUnknown*)device);
hr = D3DXCreateFontA(device, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "Arial", &font);
ok(hr == D3D_OK, "D3DXCreateFont returned %#x, expected %#x\n", hr, D3D_OK);
check_ref((IUnknown*)device, ref + 1);
check_release((IUnknown*)font, 0);
check_ref((IUnknown*)device, ref);
hr = D3DXCreateFontA(device, 0, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "Arial", &font);
ok(hr == D3D_OK, "D3DXCreateFont returned %#x, expected %#x\n", hr, D3D_OK);
ID3DXFont_Release(font);
hr = D3DXCreateFontA(device, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, NULL, &font);
ok(hr == D3D_OK, "D3DXCreateFont returned %#x, expected %#x\n", hr, D3D_OK);
ID3DXFont_Release(font);
hr = D3DXCreateFontA(device, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "", &font);
ok(hr == D3D_OK, "D3DXCreateFont returned %#x, expected %#x\n", hr, D3D_OK);
ID3DXFont_Release(font);
hr = D3DXCreateFontA(NULL, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "Arial", &font);
ok(hr == D3DERR_INVALIDCALL, "D3DXCreateFont returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = D3DXCreateFontA(device, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "Arial", NULL);
ok(hr == D3DERR_INVALIDCALL, "D3DXCreateFont returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = D3DXCreateFontA(NULL, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "Arial", NULL);
ok(hr == D3DERR_INVALIDCALL, "D3DXCreateFont returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
/* D3DXCreateFontIndirect */
desc.Height = 12;
desc.Width = 0;
desc.Weight = FW_DONTCARE;
desc.MipLevels = 0;
desc.Italic = FALSE;
desc.CharSet = DEFAULT_CHARSET;
desc.OutputPrecision = OUT_DEFAULT_PRECIS;
desc.Quality = DEFAULT_QUALITY;
desc.PitchAndFamily = DEFAULT_PITCH;
strcpy(desc.FaceName, "Arial");
hr = D3DXCreateFontIndirectA(device, &desc, &font);
ok(hr == D3D_OK, "D3DXCreateFontIndirect returned %#x, expected %#x\n", hr, D3D_OK);
ID3DXFont_Release(font);
hr = D3DXCreateFontIndirectA(NULL, &desc, &font);
ok(hr == D3DERR_INVALIDCALL, "D3DXCreateFontIndirect returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = D3DXCreateFontIndirectA(device, NULL, &font);
ok(hr == D3DERR_INVALIDCALL, "D3DXCreateFontIndirect returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = D3DXCreateFontIndirectA(device, &desc, NULL);
ok(hr == D3DERR_INVALIDCALL, "D3DXCreateFontIndirect returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
/* ID3DXFont_GetDevice */
hr = D3DXCreateFontA(device, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "Arial", &font);
if(SUCCEEDED(hr)) {
IDirect3DDevice9 *bufdev;
hr = ID3DXFont_GetDevice(font, NULL);
ok(hr == D3DERR_INVALIDCALL, "ID3DXFont_GetDevice returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
ref = get_ref((IUnknown*)device);
hr = ID3DXFont_GetDevice(font, &bufdev);
ok(hr == D3D_OK, "ID3DXFont_GetDevice returned %#x, expected %#x\n", hr, D3D_OK);
check_release((IUnknown*)bufdev, ref);
ID3DXFont_Release(font);
} else skip("Failed to create a ID3DXFont object\n");
/* ID3DXFont_GetDesc */
hr = D3DXCreateFontA(device, 12, 8, FW_BOLD, 2, TRUE, ANSI_CHARSET, OUT_RASTER_PRECIS, ANTIALIASED_QUALITY, VARIABLE_PITCH, "Arial", &font);
if(SUCCEEDED(hr)) {
hr = ID3DXFont_GetDescA(font, NULL);
ok(hr == D3DERR_INVALIDCALL, "ID3DXFont_GetDevice returned %#x, expected %#x\n", hr, D3DERR_INVALIDCALL);
hr = ID3DXFont_GetDescA(font, &desc);
ok(hr == D3D_OK, "ID3DXFont_GetDevice returned %#x, expected %#x\n", hr, D3D_OK);
ok(desc.Height == 12, "ID3DXFont_GetDesc returned font height %d, expected %d\n", desc.Height, 12);
ok(desc.Width == 8, "ID3DXFont_GetDesc returned font width %d, expected %d\n", desc.Width, 8);
ok(desc.Weight == FW_BOLD, "ID3DXFont_GetDesc returned font weight %d, expected %d\n", desc.Weight, FW_BOLD);
ok(desc.MipLevels == 2, "ID3DXFont_GetDesc returned font miplevels %d, expected %d\n", desc.MipLevels, 2);
ok(desc.Italic == TRUE, "ID3DXFont_GetDesc says Italic was %d, but Italic should be %d\n", desc.Italic, TRUE);
ok(desc.CharSet == ANSI_CHARSET, "ID3DXFont_GetDesc returned font charset %d, expected %d\n", desc.CharSet, ANSI_CHARSET);
ok(desc.OutputPrecision == OUT_RASTER_PRECIS, "ID3DXFont_GetDesc returned an output precision of %d, expected %d\n", desc.OutputPrecision, OUT_RASTER_PRECIS);
ok(desc.Quality == ANTIALIASED_QUALITY, "ID3DXFont_GetDesc returned font quality %d, expected %d\n", desc.Quality, ANTIALIASED_QUALITY);
ok(desc.PitchAndFamily == VARIABLE_PITCH, "ID3DXFont_GetDesc returned pitch and family %d, expected %d\n", desc.PitchAndFamily, VARIABLE_PITCH);
ok(strcmp(desc.FaceName, "Arial") == 0, "ID3DXFont_GetDesc returned facename \"%s\", expected \"%s\"\n", desc.FaceName, "Arial");
ID3DXFont_Release(font);
} else skip("Failed to create a ID3DXFont object\n");
/* ID3DXFont_GetDC + ID3DXFont_GetTextMetrics */
hr = D3DXCreateFontA(device, 12, 0, FW_DONTCARE, 0, FALSE, DEFAULT_CHARSET, OUT_DEFAULT_PRECIS, DEFAULT_QUALITY, DEFAULT_PITCH, "Arial", &font);
if(SUCCEEDED(hr)) {
HDC hdc;
hdc = ID3DXFont_GetDC(font);
ok(hdc != NULL, "ID3DXFont_GetDC returned an invalid handle\n");
if(hdc) {
TEXTMETRICA metrics, expmetrics;
BOOL ret;
ret = ID3DXFont_GetTextMetricsA(font, &metrics);
ok(ret, "ID3DXFont_GetTextMetricsA failed\n");
ret = GetTextMetricsA(hdc, &expmetrics);
ok(ret, "GetTextMetricsA failed\n");
ok(metrics.tmHeight == expmetrics.tmHeight, "Returned height %d, expected %d\n", metrics.tmHeight, expmetrics.tmHeight);
ok(metrics.tmAscent == expmetrics.tmAscent, "Returned ascent %d, expected %d\n", metrics.tmAscent, expmetrics.tmAscent);
ok(metrics.tmDescent == expmetrics.tmDescent, "Returned descent %d, expected %d\n", metrics.tmDescent, expmetrics.tmDescent);
ok(metrics.tmInternalLeading == expmetrics.tmInternalLeading, "Returned internal leading %d, expected %d\n", metrics.tmInternalLeading, expmetrics.tmInternalLeading);
ok(metrics.tmExternalLeading == expmetrics.tmExternalLeading, "Returned external leading %d, expected %d\n", metrics.tmExternalLeading, expmetrics.tmExternalLeading);
ok(metrics.tmAveCharWidth == expmetrics.tmAveCharWidth, "Returned average char width %d, expected %d\n", metrics.tmAveCharWidth, expmetrics.tmAveCharWidth);
ok(metrics.tmMaxCharWidth == expmetrics.tmMaxCharWidth, "Returned maximum char width %d, expected %d\n", metrics.tmMaxCharWidth, expmetrics.tmMaxCharWidth);
ok(metrics.tmWeight == expmetrics.tmWeight, "Returned weight %d, expected %d\n", metrics.tmWeight, expmetrics.tmWeight);
ok(metrics.tmOverhang == expmetrics.tmOverhang, "Returned overhang %d, expected %d\n", metrics.tmOverhang, expmetrics.tmOverhang);
ok(metrics.tmDigitizedAspectX == expmetrics.tmDigitizedAspectX, "Returned digitized x aspect %d, expected %d\n", metrics.tmDigitizedAspectX, expmetrics.tmDigitizedAspectX);
ok(metrics.tmDigitizedAspectY == expmetrics.tmDigitizedAspectY, "Returned digitized y aspect %d, expected %d\n", metrics.tmDigitizedAspectY, expmetrics.tmDigitizedAspectY);
ok(metrics.tmFirstChar == expmetrics.tmFirstChar, "Returned first char %d, expected %d\n", metrics.tmFirstChar, expmetrics.tmFirstChar);
ok(metrics.tmLastChar == expmetrics.tmLastChar, "Returned last char %d, expected %d\n", metrics.tmLastChar, expmetrics.tmLastChar);
ok(metrics.tmDefaultChar == expmetrics.tmDefaultChar, "Returned default char %d, expected %d\n", metrics.tmDefaultChar, expmetrics.tmDefaultChar);
ok(metrics.tmBreakChar == expmetrics.tmBreakChar, "Returned break char %d, expected %d\n", metrics.tmBreakChar, expmetrics.tmBreakChar);
ok(metrics.tmItalic == expmetrics.tmItalic, "Returned italic %d, expected %d\n", metrics.tmItalic, expmetrics.tmItalic);
ok(metrics.tmUnderlined == expmetrics.tmUnderlined, "Returned underlined %d, expected %d\n", metrics.tmUnderlined, expmetrics.tmUnderlined);
ok(metrics.tmStruckOut == expmetrics.tmStruckOut, "Returned struck out %d, expected %d\n", metrics.tmStruckOut, expmetrics.tmStruckOut);
ok(metrics.tmPitchAndFamily == expmetrics.tmPitchAndFamily, "Returned pitch and family %d, expected %d\n", metrics.tmPitchAndFamily, expmetrics.tmPitchAndFamily);
ok(metrics.tmCharSet == expmetrics.tmCharSet, "Returned charset %d, expected %d\n", metrics.tmCharSet, expmetrics.tmCharSet);
}
ID3DXFont_Release(font);
} else skip("Failed to create a ID3DXFont object\n");
}
int main(int argc, char **argv)
{
cl_int err = 0;
cl_context context = 0;
cl_device_id * devices = NULL;
cl_command_queue queue = 0;
cl_program program = 0;
cl_mem cl_a = 0, cl_b = 0, cl_res = 0;
cl_kernel adder = 0;
cl_event event;
// The iteration variable
int i;
// Define our data set
cl_float a[DATA_SIZE], b[DATA_SIZE], res[DATA_SIZE];
// Initialize array
srand(time(0));
for (i = 0; i < DATA_SIZE; i++) {
a[i] = (rand() % 100) / 100.0;
b[i] = (rand() % 100) / 100.0;
res[i] = 0;
}
check_release(get_cl_context(&context, &devices, 0) == false,
"Fail to create context");
// Specify the queue to be profile-able
queue = clCreateCommandQueue(context, devices[0], CL_QUEUE_PROFILING_ENABLE, 0);
check_release(queue == NULL, "Can't create command queue");
program = load_program(context, devices[0], "shader.cl");
check_release(program == NULL, "Fail to build program");
cl_a =
clCreateBuffer(context, CL_MEM_READ_ONLY, sizeof(cl_float) * DATA_SIZE, NULL, NULL);
cl_b =
clCreateBuffer(context, CL_MEM_READ_ONLY, sizeof(cl_float) * DATA_SIZE, NULL, NULL);
cl_res = clCreateBuffer(
context, CL_MEM_WRITE_ONLY, sizeof(cl_float) * DATA_SIZE, NULL, NULL);
if (cl_a == 0 || cl_b == 0 || cl_res == 0) {
printf("Can't create OpenCL buffer\n");
goto release;
}
check_release(clEnqueueWriteBuffer(
queue, cl_a, CL_TRUE, 0, sizeof(cl_float) * DATA_SIZE, a, 0, 0, 0),
"Write Buffer 1");
check_release(clEnqueueWriteBuffer(
queue, cl_b, CL_TRUE, 0, sizeof(cl_float) * DATA_SIZE, b, 0, 0, 0),
"Write Buffer 2");
adder = clCreateKernel(program, "adder", &err);
if (err == CL_INVALID_KERNEL_NAME) printf("CL_INVALID_KERNEL_NAME\n");
check_release(adder == NULL, "Can't load kernel");
clSetKernelArg(adder, 0, sizeof(cl_mem), &cl_a);
clSetKernelArg(adder, 1, sizeof(cl_mem), &cl_b);
clSetKernelArg(adder, 2, sizeof(cl_mem), &cl_res);
size_t work_size = DATA_SIZE;
check_release(clEnqueueNDRangeKernel(queue, adder, 1, 0, &work_size, 0, 0, 0, &event),
"Can't enqueue kernel");
check_release(
clEnqueueReadBuffer(
queue, cl_res, CL_TRUE, 0, sizeof(cl_float) * DATA_SIZE, res, 0, 0, 0),
"Can't enqueue read buffer");
clWaitForEvents(1, &event);
printf("Execution Time: %.04lf ms\n\n", get_event_exec_time(event));
// Make sure everything is done before we do anything
clFinish(queue);
err = 0;
for (i = 0; i < DATA_SIZE; i++) {
if (res[i] != a[i] + b[i]) {
printf("%f + %f = %f(answer %f)\n", a[i], b[i], res[i], a[i] + b[i]);
err++;
}
}
if (err == 0)
printf("Validation passed\n");
else
printf("Validation failed\n");
printf("------\n");
//--------------------------------
// Second test
for (i = 0; i < DATA_SIZE; i++) {
a[i] = i;
b[i] = i;
res[i] = 0;
}
check_err(clEnqueueWriteBuffer(
queue, cl_a, CL_TRUE, 0, sizeof(cl_float) * DATA_SIZE, a, 0, 0, 0),
"Write Buffer 1");
check_err(clEnqueueWriteBuffer(
queue, cl_b, CL_TRUE, 0, sizeof(cl_float) * DATA_SIZE, b, 0, 0, 0),
"Write Buffer 2");
check_err(clEnqueueNDRangeKernel(queue, adder, 1, 0, &work_size, 0, 0, 0, &event),
"Can't enqueue kernel");
check_err(clEnqueueReadBuffer(
queue, cl_res, CL_TRUE, 0, sizeof(cl_float) * DATA_SIZE, res, 0, 0, 0),
"Can't enqueue read buffer");
clWaitForEvents(1, &event);
printf("Execution Time: %.04lf ms\n\n", get_event_exec_time(event));
// Make sure everything is done before we do anything
clFinish(queue);
err = 0;
for (i = 0; i < DATA_SIZE; i++) {
if (res[i] != a[i] + b[i]) {
printf("%f + %f = %f(answer %f)\n", a[i], b[i], res[i], a[i] + b[i]);
err++;
}
}
if (err == 0)
printf("Validation passed\n");
else
printf("Validation failed\n");
release:
clReleaseKernel(adder);
clReleaseProgram(program);
clReleaseMemObject(cl_a);
clReleaseMemObject(cl_b);
clReleaseMemObject(cl_res);
clReleaseCommandQueue(queue);
clReleaseContext(context);
return 0;
}
