Commit Graph

304 Commits

Author SHA1 Message Date
Alexey Spizhevoy
2f8af6335e renamed GpuFeature into FeatureSet and updated docs 2011-02-15 13:56:59 +00:00
Alexey Spizhevoy
04709a2793 refactoring of GPU module 2011-02-15 13:25:24 +00:00
Anatoly Baksheev
6b6a63ba38 fixed some warnings
GPU: TargetArchs -> added FEATURE_SET prefix.
2011-02-15 10:54:49 +00:00
Alexey Spizhevoy
725d83b0e5 added init() function into MultiGpuMgr, added samples 2011-02-15 10:03:26 +00:00
Alexey Spizhevoy
5d4913a2ee fixed multi GPU API, added driver_api prefix to multi gpu samples 2011-02-15 09:12:48 +00:00
Vladislav Vinogradov
deac5d972e fixed errors in gpu on old video cards (SURF_GPU, BruteForceMatcher_GPU, min/max, setTo, convertTo)
added assertion after all kernels calls
2011-02-14 15:50:17 +00:00
Alexey Spizhevoy
a42a42858c fixed GPU samples and MultiGpuMgr 2011-02-14 15:09:45 +00:00
Alexey Spizhevoy
186e46fcca added draft version of MultiGpuMgr (it isn't tested on multi GPU machine yet) 2011-02-14 12:53:59 +00:00
Alexey Spizhevoy
63806c9ab9 renamed gpu::DeviceInfo::has into gpu::DeviceInfo::supports 2011-02-09 12:31:05 +00:00
Alexey Spizhevoy
50429d8a3e fixed some warnings and errors under g++ 2011-02-03 14:51:58 +00:00
Alexey Spizhevoy
557dd39f03 fixed gpu::sum* on CC1.0, updated some tests 2011-02-02 07:23:55 +00:00
Alexey Spizhevoy
16e74ab306 added buffered version of norm, updated performance sample and docs 2011-02-01 10:46:19 +00:00
Alexey Spizhevoy
ae529f4bc6 added absSum function 2011-01-31 14:37:03 +00:00
Vladislav Vinogradov
8274ed22e4 fixed gpu tests (BruteForceMatcher_GPU, divide, phase, cartToPolar, async)
minor code refactoring
2011-01-31 13:20:52 +00:00
Alexey Spizhevoy
7a29d96cf4 added buffered version of gpu::integral function and updated performance test (it still works too slow) 2011-01-31 10:42:33 +00:00
Alexey Spizhevoy
575fd1fe4c reafactoring: replaced query device props functions with the DeviceInfo class 2011-01-28 11:59:26 +00:00
Alexey Spizhevoy
891e2ff310 replaced has* methods in the GPU module with the TargetArchs monostate 2011-01-27 10:06:38 +00:00
Vladislav Vinogradov
eda8416358 fixed BruteForceMatcher_GPU (fails if input data is empty)
updated BruteForceMatcher_GPU test
2011-01-26 15:58:47 +00:00
Vladislav Vinogradov
8abdb3721f added gpu threshold. 2011-01-24 10:11:02 +00:00
Alexey Spizhevoy
8779306800 updated main CMakeLists.txt gpu module section, now user can manage binary and intermediate code versions of the gpu module image
added more functions to check version of gpu code in runtime
2011-01-20 09:22:05 +00:00
Alexey Spizhevoy
90ae1e3aed refactored gpu module 2011-01-19 10:54:58 +00:00
Alexey Spizhevoy
1a0d41fb53 added checkPtxVersion into gpu module 2011-01-18 14:52:35 +00:00
Alexey Spizhevoy
cbb132ccb1 added ensureSizeIsEnough into gpu module, updated reduction methods 2011-01-18 12:36:01 +00:00
Alexey Spizhevoy
f3a2656808 added hasPtxFor and isCompatibleWith functions into gpu module, added docs for them 2011-01-18 12:01:28 +00:00
Alexey Spizhevoy
db852e0b54 updated gpu module docs 2011-01-13 13:55:13 +00:00
Vladislav Vinogradov
349e0ece93 added docs for GPU Filter Engine 2011-01-13 13:48:58 +00:00
Anatoly Baksheev
1a94186195 First version of CascadeClassifier_GPU.
Only for VS2008 now.
Sample for it.
new NPP_staging for VS2008 only
2011-01-13 13:04:00 +00:00
Alexey Spizhevoy
4dfbf99dd5 cosmetic changes in gpu module, decreased matchTemplate test running time 2011-01-12 09:30:08 +00:00
Alexey Spizhevoy
dc763e0250 updated normalization routine in the matchTemplate to avoid division by zero on black images (ticket #798), added test 2011-01-11 09:36:21 +00:00
Alexey Spizhevoy
2f13e4ce58 refactored hog, added camera support into hog_sample 2010-12-29 15:45:01 +00:00
Alexey Spizhevoy
be38864dd0 added buffered version of gpu::convolve 2010-12-27 10:18:42 +00:00
Alexey Spizhevoy
8f0d36b8b6 refactored gpu::dft 2010-12-27 07:35:41 +00:00
Alexey Spizhevoy
21b081deff now single row GPU matrix is continuous one, added aux. functions, updated dft and matchTemplates 2010-12-24 09:26:19 +00:00
Alexey Spizhevoy
54fcdf4cae minor changes in gpu module (comments and warnings) 2010-12-24 07:00:08 +00:00
Alexey Spizhevoy
09735fd208 added gpu::dft implemented via CUFFT 2010-12-23 09:24:33 +00:00
Alexey Spizhevoy
68aba9f2fb added mulSpectrums functions into GPU module 2010-12-22 13:46:06 +00:00
Alexey Spizhevoy
fef06c25b5 moved crossCorr (as NPP_Staging wrapper) into public GPU module part from the internal matchTemplate files 2010-12-22 08:56:16 +00:00
Alexey Spizhevoy
f9bcef9003 moved sqrIntegral (NPP_Staging wrapper) into public GPU module part from matchTemplate.cpp 2010-12-22 08:17:36 +00:00
Vladislav Vinogradov
0cd587ee34 added gpu transpose and integral based on NPP Staging.
added mask support to SURF_GPU.
2010-12-21 14:02:09 +00:00
Vladislav Vinogradov
0e45a637c4 added SURF_GPU.
added support of CV_32FC1 type to gpu copyMakeBorder.
2010-12-20 12:49:40 +00:00
Alexey Spizhevoy
df8529377b refactoring: moved gpu reduction-based functions into separated file 2010-12-20 09:51:25 +00:00
Alexey Spizhevoy
1922e50f19 refactoring: made gpu bitwise operations inline 2010-12-20 09:16:17 +00:00
Alexey Spizhevoy
0465b89e7e gpu module refactoring: moved per-element operations into separated file 2010-12-20 09:07:19 +00:00
Anatoly Baksheev
9dd4a22a5e temporary added NPP_staging, functionality from the library will be moved to NPP with next release. 2010-12-17 15:41:26 +00:00
Alexey Spizhevoy
a81b41fb08 fixed some warning under Ubuntu in gpu module 2010-12-13 15:56:29 +00:00
Alexey Spizhevoy
c9f9f38777 added gpu::sqrSum function 2010-12-13 14:34:02 +00:00
Alexey Spizhevoy
3997514b7c added tests for gpu::sum, it supports all data types, but single channel images only 2010-12-13 12:00:58 +00:00
Vladislav Vinogradov
49ec8ba742 fixed bug in gpu filter engine (incorrect buffer type) and in vector's saturate_cast.
changed buffer type in linear filters to float.
added support of 1 channel image to linear filters.
added support of BORDER_REFLECT101, BORDER_REPLICATE and BORDER_CONSTANT border type to gpu linear filters.
minor fix in tests.
update comments in gpu.hpp.
2010-12-13 08:43:04 +00:00
Alexey Spizhevoy
d557c800a7 refactored gpu module 2010-12-10 10:23:32 +00:00
Alexey Spizhevoy
fa322bf46f added gpu::columnSum, fixed compile error (if there is no cuda), refactored 2010-12-08 15:06:10 +00:00
Alexey Spizhevoy
19b434be50 minor refactoring of gpu module 2010-12-07 06:45:54 +00:00
Anatoly Baksheev
652fb1212e module reorganization: added folder with pure device functions, cuda_shared.hpp renamed to internal_shared.hpp 2010-12-06 16:37:32 +00:00
Alexey Spizhevoy
50167f6c26 added first version of gpu::matchTemplate, currently it works only with 8UC1 images and SQDIFF method 2010-12-06 14:19:41 +00:00
Vladislav Vinogradov
8891acb67a added BruteForceMatcher_GPU 2010-12-06 12:06:51 +00:00
Vladislav Vinogradov
17d9014373 added per-element min/max to gpu module.
fixed compile error in transform.
2010-12-06 08:10:11 +00:00
Alexey Spizhevoy
df48ad76b0 added support of gamama_correction parameter into gpu::HOGDescriptor, updated tests 2010-12-03 11:11:44 +00:00
Alexey Spizhevoy
ab04a03621 added support of BORDER_REFLECT into gpu::cornerHarris and etc, added support of border extr. int linear filters 2010-12-02 09:07:13 +00:00
Alexey Spizhevoy
493d7a6e45 added min eigen val based corner detector into gpu module 2010-11-30 08:44:04 +00:00
Alexey Spizhevoy
9adfc2cadc added Harris corner detector into gpu module 2010-11-30 08:04:37 +00:00
Alexey Spizhevoy
b260382840 added masks support into gpu::minMaxLoc 2010-11-29 13:56:43 +00:00
Alexey Spizhevoy
437ac1a2f1 added mask support into gpu::minMax 2010-11-29 10:29:21 +00:00
Alexey Spizhevoy
72f020a8f3 added gpu::count_non_zero version for CC1.0, refactored gpu module a little 2010-11-29 07:18:11 +00:00
Alexey Spizhevoy
7e2cc1be1b added first version of gpu::countNonZero for all data types, it doesn't support compute capability 1.0 yet, also fixed some little bugs 2010-11-26 17:12:48 +00:00
Alexey Spizhevoy
bdaad9e1fe added support of buffers into gpu::minMaxLoc, reduced memory requirements, refactored 2010-11-26 07:50:11 +00:00
Alexey Spizhevoy
fa5422a2ad added buf support into gpu::minMax 2010-11-25 10:19:06 +00:00
Alexey Spizhevoy
27690e3b6e added minMaxLoc function into gpu module 2010-11-24 11:40:14 +00:00
Alexey Spizhevoy
282e01cb4a added support of all data types into gpu::minMax 2010-11-24 08:55:52 +00:00
Alexey Spizhevoy
732bd621bb added masks support for bitwise operations on GPU 2010-11-22 09:39:34 +00:00
Andrey Morozov
680dc71bc5 fixed compilation error and warnings under ubuntu 2010-11-20 14:41:28 +00:00
Alexey Spizhevoy
6a9d022a9f added support of different descriptor formats into gpu HOGDescriptor 2010-11-19 12:06:11 +00:00
Alexey Spizhevoy
faf4d0bc74 added bitwise operations into gpu module 2010-11-19 10:19:35 +00:00
Alexey Spizhevoy
11c0c5bf85 added getDescriptors support into gpu HOG, also added commented test for this feature 2010-11-18 09:22:23 +00:00
Alexey Spizhevoy
8adc62016b added getDescriptors function (draft version) 2010-11-17 17:10:23 +00:00
Alexey Spizhevoy
4568d702ff added getPeopleDetector_48x96 into gpu HOG 2010-11-17 08:31:24 +00:00
Anatoly Baksheev
edff674105 added default detector for winSize(64,128) for hog on gpu 2010-11-16 12:33:19 +00:00
Vladislav Vinogradov
be54f1237a minor fix 2010-11-16 07:40:37 +00:00
Anatoly Baksheev
f2df784830 fixed error reporting in GPU module (exceptions in destructors, etc) 2010-11-15 16:22:52 +00:00
Alexey Spizhevoy
fada88e100 fixed some bugs, added tests for gpu::HOGDescriptor 2010-11-15 12:51:30 +00:00
Alexey Spizhevoy
13134595fd added HOGDescriptor on GPU 2010-11-15 11:01:56 +00:00
Anatoly Baksheev
55a722fc9d some utility for GPU module internal purposes 2010-11-10 17:05:36 +00:00
Anatoly Baksheev
c923b258f4 fixed compilation under gcc 2010-11-01 15:13:17 +00:00
Anatoly Baksheev
7f56e5b2dd compilation errors 2010-11-01 12:49:45 +00:00
Anatoly Baksheev
4ea811c568 Fixed a minor bug in PtrElemStep::ptr 2010-11-01 12:48:47 +00:00
Anatoly Baksheev
cac2e9bc80 compilation errors under GCC 2010-10-31 17:15:09 +00:00
Anatoly Baksheev
d661b8e3e2 added PtrStep PtrElemStep structures. Refactored name spaces, 2010-10-31 13:23:25 +00:00
Vladislav Vinogradov
2c39f0ee33 fix unnecessary memory allocation in gpu::magnitude and gpu::phase 2010-10-26 05:44:50 +00:00
Anatoly Baksheev
5ac4b23b7c added PtrStep structure to pass in __global__ functions 2010-10-22 16:57:22 +00:00
Vladislav Vinogradov
b08f60828b added to gpu module linear filters for int and float source types.
refactored gpu module.
2010-10-20 08:50:14 +00:00
Vladislav Vinogradov
e12e4798e0 added gpu version of magnitude, magnitudeSqr, phase, cartToPolar, polarToCart 2010-10-18 11:12:14 +00:00
Vladislav Vinogradov
4124633359 added magnitudeSqr and rectStdDev to gpu module.
added supports of CV_32SC2 source to gpu scalar arithm and float source to gpu::histRange.
minor fix of gpu tests.
2010-10-13 12:52:39 +00:00
Alexey Spizhevoy
970dd7f593 implemented mean shift segmentation with elimination of small segments, added tests 2010-10-13 09:10:24 +00:00
Vladislav Vinogradov
f6895e7738 fixed gpu filters (deriv filter and source roi calculation) 2010-10-12 08:33:06 +00:00
Vladislav Vinogradov
ced60b7498 added histograms calculation to gpu module 2010-10-12 06:37:44 +00:00
Alexey Spizhevoy
adf7cc20b7 changed mean shift procedure a little 2010-10-11 14:25:30 +00:00
Vladislav Vinogradov
3e840cb798 added min/max filters to gpu module.
added supports of 4-channels image to gpu::minMax and gpu::cvtColor for RGB <-> YCrCB, RGB <-> YUV and RGB <-> XYZ color conversion.
2010-10-11 08:54:28 +00:00
Vladislav Vinogradov
66df8ef06c added Filter Engine to gpu module.
disabled gpu::sum, gpu::minMax, gpu:Canny until fix crash.
2010-10-06 14:32:13 +00:00
Vladislav Vinogradov
49fa536c62 added Sobel, GaussianBlur, Canny to gpu module.
minor fix of matrix_operations.cpp.
2010-10-04 11:42:40 +00:00
Vladislav Vinogradov
fb7aa43feb added gpu 1d window sum, convertTo, based on NPP.
added RGB <-> XYZ color conversion.
gpu morphology minor fix.
2010-09-29 09:07:53 +00:00
Anatoly Baksheev
60e572bbcf fixed gpu morphology: now kernel in gpu is passed to npp functions.
warnings in cxcore
added graphcut wrapper
2010-09-28 08:45:44 +00:00
Vladislav Vinogradov
5285722c1c added gpu::magnitude for complex source vector (two channels float).
added gpu::cvtColor for BGR5x5 <-> BGR and BGR5x5 <-> Gray.
2010-09-27 14:10:19 +00:00
Alexey Spizhevoy
992485c532 updated StereoBP docs & comments 2010-09-27 13:30:50 +00:00
Vladislav Vinogradov
51d5959aca added gpu add, subtract, multiply, divide, absdiff with Scalar.
added gpu exp, log, magnitude, based on NPP.
updated setTo with new NPP functions.
minor fix in tests and comments.
2010-09-27 12:44:57 +00:00
Anatoly Baksheev
a5910ac068 modified according to NPP for CUDA 3.2 API updates. 2010-09-24 16:41:34 +00:00
Vladislav Vinogradov
4100cbd997 added gpu version of LUT, integral, boxFilter and cvtColor (RGB <-> YCrCb), based on NPP.
minor refactoring of GPU module and GPU tests, split arithm and imgproc parts.
2010-09-22 10:58:01 +00:00
Alexey Spizhevoy
b2cdb7fa39 implemented cv::gpu::merge and cv::gpu::split functions 2010-09-20 13:20:25 +00:00
Vladislav Vinogradov
a2f8817df1 minor refactoring of GPU module and GPU tests
added gpu compare version for CMP_NE operation
2010-09-20 10:34:46 +00:00
Anatoly Baksheev
4ffb519cdd GPU module: minor interface changes 2010-09-17 17:18:41 +00:00
Anatoly Baksheev
1387bfcde0 added GPU implementation of morphology functions (using NPP) and tests for it.
added npp_error function
added check_and_treat_gpu_exception function for tests_gpu
2010-09-17 15:28:59 +00:00
Vladislav Vinogradov
b181d78ca5 Added implementation and test for the GPU version of warpAffine, warpPerspective, rotate, based on NPP.
Renamed copyConstBorder to copyMakeBorder.
Fixed warnings when HAVE_CUDA is not defined.
2010-09-15 12:47:59 +00:00
Vladislav Vinogradov
b5c92a7dc0 Added implementation and test for the GPU version of flip, resize, sum, minMax, copyConstBorder, setTo, based on NPP. 2010-09-15 08:26:18 +00:00
Vladislav Vinogradov
37d39bd9de Added implementation and test for the GPU version of subtract, multiply, divide, transpose, absdiff, threshold, compare, meanStdDev, norm, based on NPP. 2010-09-13 14:30:09 +00:00
Kirill Kornyakov
01eac6d3e3 Added initial implementation and test for the GPU version of add, based on NPP. Need to implement for other depths. Also waiting NPP at CMake. 2010-09-09 15:34:16 +00:00
Kirill Kornyakov
6960e1544d GPU module update: _GPU suffix removed, some namespaces renamed, minor refactorings. 2010-09-06 14:27:23 +00:00
Kirill Kornyakov
ec7e937481 meanShiftFiltering_GPU output parameters changed to CV_8UC4. This is a start for moving from 3 channel to C4 images within GPU module. 2010-09-03 14:32:12 +00:00
Vladislav Vinogradov
0a73af8e22 added cvtColor on gpu (supports conversion between RGB, BGR and GRAY) 2010-08-30 13:41:26 +00:00
Vladislav Vinogradov
304caab746 added remap version for 3-channels input images 2010-08-26 09:19:47 +00:00
Andrey Morozov
096080de70 added methods estimateRecopmmendedParams for StereoBP and StereoCSBP 2010-08-25 07:27:17 +00:00
Vladislav Vinogradov
1febf345bf renamed colorizeDisp to drawColorDisp, added acync version of drawColorDisp and reprojectImageTo3D_GPU. 2010-08-25 06:30:11 +00:00
Vladislav Vinogradov
ec4ce050f9 added reprojectImageTo3D_GPU 2010-08-23 14:19:22 +00:00
Vladislav Vinogradov
6cafec8861 added colorizeDisp, fixed DisparityBilateralFilter 2010-08-20 06:47:11 +00:00
Vladislav Vinogradov
1f04ea477f added DisparityBilateralFilter to gpu module 2010-08-19 08:44:06 +00:00
Anatoly Baksheev
97d17d8ad1 fixed warnings
added comments in gpu.hpp
2010-08-18 17:13:01 +00:00
Andrey Morozov
aaa8678cff fixed some warnings 2010-08-18 13:47:10 +00:00
Andrey Morozov
28030952fa added get_first_k_initial_global_init_global_cost in gpu::SCBP 2010-08-17 15:53:00 +00:00
Anatoly Baksheev
9a669b1ceb fixed bugs in page locked memory allocation
avoid extra gpu memory allocation in BP and CSBP
2010-08-17 10:39:18 +00:00
Vladislav Vinogradov
9ddb373614 added version of StereoBeliefPropagation::operator() for user specified data term 2010-08-16 14:47:17 +00:00
Anatoly Baksheev
4c4871e34d GCC warning: new line at the end of file 2010-08-16 08:47:06 +00:00
Anatoly Baksheev
ef9a9d43a4 a lot of refactoring 2010-08-13 16:50:07 +00:00
Andrey Morozov
35ebeb21bd added implement MatPL with serocopy and writecombited 2010-08-13 14:52:50 +00:00
Anatoly Baksheev
77ce659154 2010-08-13 12:51:55 +00:00
Vladislav Vinogradov
6062fad7d8 added minimum disparity threshold parameter to StereoConstantSpaceBP 2010-08-13 11:17:51 +00:00
Vladislav Vinogradov
26712fad72 gpu::StereoConstantSpaceBP:
fixed some bugs in init_data_cost on first level (added non-reduction version for first level)
  optimized compute_data_cost like init_data_cost (used reduction scheme)
  avoid temp matrix
2010-08-13 08:30:06 +00:00
Vladislav Vinogradov
ee104c27d8 added gpu implementation of constant space belief propagation stereo matching.
some refactoring of StereoBeliefPropagation.
2010-08-12 12:15:37 +00:00
Anatoly Baksheev
2a385be0ef meanShiftFilteringGPU: performance and bug with type conversions 2010-08-10 12:18:47 +00:00
Anatoly Baksheev
d1fc3e6b5a cv::gpu::CudaStream -> cv::gpu::Stream
some refactoring
added gpu module to compilation
2010-08-10 09:44:50 +00:00
Anatoly Baksheev
9ee159462d meanShiftFiltering added (by masha)
get free memory function
2010-08-06 17:02:06 +00:00
Vladislav Vinogradov
788ac96f8b added optimized belief propagation implementation (used short for messages) 2010-08-02 11:10:29 +00:00
Anatoly Baksheev
9ac1741555 speckle filtering added 2010-07-29 08:50:19 +00:00
Vladislav Vinogradov
63fed0f831 changed StereoBeliefPropagation_GPU output disparity default type to CV_32S 2010-07-29 08:47:06 +00:00
Vladislav Vinogradov
84f51332dd implemented asynchronous call for StereoBeliefPropagation_GPU 2010-07-29 07:20:35 +00:00
Vladislav Vinogradov
5bd128fac8 added gpu belief propagation stereo matching 2010-07-28 14:46:44 +00:00
Andrey Morozov
12dc52c2e7 implemented asynchronous call for StereoBM() 2010-07-27 08:29:40 +00:00
Anatoly Baksheev
22f5376e82 refactoring and minor code improvements
added cuda_shared.hpp header was reorganized in order to speed up compilation
2010-07-26 15:04:56 +00:00
Andrey Morozov
fff2160d1f implemented asynchronous call for GpuMat::upload() and GpuMat::download(). added test for asynchronous call. 2010-07-26 13:42:39 +00:00
Andrey Morozov
769564c130 implemented asynchronous call for gpumat::setTo(), gpumat::copyTo(), gpumat::converTo() 2010-07-26 11:22:16 +00:00
Anatoly Baksheev
d352db7ec4 imgproc_gpu - minor refactoring 2010-07-23 15:04:16 +00:00
Vladislav Vinogradov
edd68e588b Added implementation of remap on GPU. Minor fixes of convertTo. Added opencv_imgproc to gpu_test dependencies. 2010-07-23 07:06:33 +00:00
Anatoly Baksheev
17f7b12a83 Variable winSize for StereoBP_GPU
Fixed StereoBM_GPU kernel crash
Textureness threshold added
2010-07-22 15:32:03 +00:00
Anatoly Baksheev
f31cf6d88d prefilter_xsobel option added to stereobm_gpu 2010-07-20 13:00:07 +00:00
Andrey Morozov
ace7c7e93c linux compiletion error 2010-07-19 10:49:35 +00:00
Anatoly Baksheev
07825bad1e compilation with no cuda re factored 2010-07-19 09:31:12 +00:00
Anatoly Baksheev
2c84a66ec7 added support to build without cuda. 2010-07-15 13:36:00 +00:00
Anatoly Baksheev
c4ef619ac5 minor changes in gpu code (initialization interface) 2010-07-15 09:13:15 +00:00
Anatoly Baksheev
7f6fb6ef97 First gpu code draft. Interface might be significantly changed in future.
Simple implementation of StereoBM_GPU.
It is excluded from compilation now.
2010-07-14 15:55:16 +00:00