Ask Your Question

Revision history [back]

click to hide/show revision 1
initial version

asked 2014-03-17 14:05:25 -0600

我干过豪哥 gravatar image

a wierd result of a project with GpuMat and cuda

enter code here#include <opencv2/core/core.hpp>

include <opencv2 gpu="" gpu.hpp="">

include <opencv2 core="" cuda_devptrs.hpp="">

include <opencv2 gpu="" stream_accessor.hpp="">

include <opencv2 gpu="" device="" common.hpp="">

include <opencv2 highgui="" highgui.hpp="">

include <iostream>

include <cuda_runtime.h>

using namespace std; using namespace cv; using namespace cv::gpu;

__global__ void AddColor_Kernel(const PtrStepSz<uchar3> src,const PtrStepSz<uchar> mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask) { int x = blockIdx.x * blockDim.x + threadIdx.x; int y = blockIdx.y * blockDim.y + threadIdx.x;

if(y < mask.rows && x < mask.cols)
{
    if(mask(y,x))
        dst.ptr(y )[ x] = src.ptr(y)[x];
    dst_mask.ptr(y )[ x] |= mask.ptr(y)[x];
}

}

void AddColorCaller(const PtrStepSz<uchar3> &src,const PtrStepSz<uchar> &mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask,cudaStream_t stream) {

dim3 block(32,8);
//  dim3 grid(divUp(src.cols ,block.x),divUp(src.rows ,block.y));
dim3 grid((mask.cols + block.x - 1)/block.x,(mask.rows + block.y - 1)/block.y);
AddColor_Kernel<<<grid,block,0,stream>>>(src,mask,dst,dst_mask);
cudaSafeCall(cudaGetLastError());
if(stream == 0)
    cudaSafeCall(cudaDeviceSynchronize());

}

void AddColor(const GpuMat &src,const GpuMat &mask, GpuMat &dst, GpuMat &dst_mask,Stream& stream = Stream::Null()) {
dst.create(src.size(),src.type()); dst.setTo(Scalar::all(0)); dst_mask.create(mask.size(),mask.type()); dst_mask.setTo(Scalar::all(0)); cudaStream_t st = StreamAccessor::getStream(stream); AddColorCaller(src,mask,dst,dst_mask,st); }

int main() { Mat image = imread("1.jpg"); Mat mask = imread("mask.jpg",-1); cout<<mask.channels()&lt;<endl; resize(mask,mask,image.size());<="" p=""> 

imshow("src",image);
imshow("mask",mask);
GpuMat gpuMat,output,mask_gpu,dst,dst_mask;

gpuMat.upload(image);
mask_gpu.upload(mask);
AddColor(gpuMat,mask_gpu,dst,dst_mask);
namedWindow("1",CV_WINDOW_OPENGL);
imshow("1",dst);
waitKey(0); 
return 0;

}

a wierd result of a project with GpuMat and cuda

enter 
The code here#include <opencv2/core/core.hpp>
as following:

include <opencv2 core="" core.hpp="">

include <opencv2 gpu="" gpu.hpp="">

include <opencv2 core="" cuda_devptrs.hpp="">

include <opencv2 gpu="" stream_accessor.hpp="">

include <opencv2 gpu="" device="" common.hpp="">

include <opencv2 highgui="" highgui.hpp="">

include <iostream>

include <cuda_runtime.h>

using namespace std; using namespace cv; using namespace cv::gpu;

__global__ void AddColor_Kernel(const PtrStepSz<uchar3> src,const PtrStepSz<uchar> mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask) { int x = blockIdx.x * blockDim.x + threadIdx.x; int y = blockIdx.y * blockDim.y + threadIdx.x;

if(y < mask.rows && x < mask.cols)
{
    if(mask(y,x))
        dst.ptr(y )[ x] = src.ptr(y)[x];
    dst_mask.ptr(y )[ x] |= mask.ptr(y)[x];
}

}

void AddColorCaller(const PtrStepSz<uchar3> &src,const PtrStepSz<uchar> &mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask,cudaStream_t stream) {

dim3 block(32,8);
//  dim3 grid(divUp(src.cols ,block.x),divUp(src.rows ,block.y));
dim3 grid((mask.cols + block.x - 1)/block.x,(mask.rows + block.y - 1)/block.y);
AddColor_Kernel<<<grid,block,0,stream>>>(src,mask,dst,dst_mask);
cudaSafeCall(cudaGetLastError());
if(stream == 0)
    cudaSafeCall(cudaDeviceSynchronize());

}

void AddColor(const GpuMat &src,const GpuMat &mask, GpuMat &dst, GpuMat &dst_mask,Stream& stream = Stream::Null()) {
dst.create(src.size(),src.type()); dst.setTo(Scalar::all(0)); dst_mask.create(mask.size(),mask.type()); dst_mask.setTo(Scalar::all(0)); cudaStream_t st = StreamAccessor::getStream(stream); AddColorCaller(src,mask,dst,dst_mask,st); }

int main() { Mat image = imread("1.jpg"); Mat mask = imread("mask.jpg",-1); cout<<mask.channels()&lt;<endl; resize(mask,mask,image.size());<="" p=""> 

imshow("src",image);
imshow("mask",mask);
GpuMat gpuMat,output,mask_gpu,dst,dst_mask;

gpuMat.upload(image);
mask_gpu.upload(mask);
AddColor(gpuMat,mask_gpu,dst,dst_mask);
namedWindow("1",CV_WINDOW_OPENGL);
imshow("1",dst);
waitKey(0); 
return 0;

}

click to hide/show revision 3
No.3 Revision

updated 2014-03-17 14:08:44 -0600

berak gravatar image

a wierd weird result of a project with GpuMat and cuda

The code as following:

include <opencv2 core="" core.hpp="">

include <opencv2 gpu="" gpu.hpp="">

include <opencv2 core="" cuda_devptrs.hpp="">

include <opencv2 gpu="" stream_accessor.hpp="">

include <opencv2 gpu="" device="" common.hpp="">

include <opencv2 highgui="" highgui.hpp="">

include <iostream>

include <cuda_runtime.h>

#include <opencv2/core/core.hpp>
#include <opencv2/gpu/gpu.hpp>
#include <opencv2/core/cuda_devptrs.hpp>
#include <opencv2/gpu/stream_accessor.hpp>
#include <opencv2/gpu/device/common.hpp>  
#include <opencv2/highgui/highgui.hpp>
#include <iostream>
#include <cuda_runtime.h>
using namespace std;
using namespace cv;
using namespace cv::gpu;
 
cv::gpu;
__global__ void AddColor_Kernel(const PtrStepSz<uchar3> src,const PtrStepSz<uchar> mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask)
{
int x = blockIdx.x * blockDim.x + threadIdx.x;
int y = blockIdx.y * blockDim.y + threadIdx.x;
 
threadIdx.x;
if(y < mask.rows && x < mask.cols)
 {
 if(mask(y,x))
  dst.ptr(y )[ x] = src.ptr(y)[x];
  dst_mask.ptr(y )[ x] |= mask.ptr(y)[x];
}

 
}
 
 }
}
void AddColorCaller(const PtrStepSz<uchar3> &src,const PtrStepSz<uchar> &mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask,cudaStream_t stream)
{
 
{
dim3 block(32,8);
 // dim3 grid(divUp(src.cols ,block.x),divUp(src.rows ,block.y));
 dim3 grid((mask.cols + block.x - 1)/block.x,(mask.rows + block.y - 1)/block.y);
 AddColor_Kernel<<<grid,block,0,stream>>>(src,mask,dst,dst_mask);
 cudaSafeCall(cudaGetLastError());
 if(stream == 0)
 cudaSafeCall(cudaDeviceSynchronize());

 
}
 
}
void AddColor(const GpuMat &src,const GpuMat &mask, GpuMat &dst, GpuMat &dst_mask,Stream& stream = Stream::Null())
{ 
 
dst.create(src.size(),src.type());
dst.setTo(Scalar::all(0));
dst_mask.create(mask.size(),mask.type());
dst_mask.setTo(Scalar::all(0));
cudaStream_t st = StreamAccessor::getStream(stream);
AddColorCaller(src,mask,dst,dst_mask,st);
}
 
}
int main()
{
Mat image = imread("1.jpg");
Mat mask = imread("mask.jpg",-1);
cout<<mask.channels()&lt;<endl; resize(mask,mask,image.size());<="" p="">

cout<<mask.channels()<<endl;
resize(mask,mask,image.size());
imshow("src",image);
 imshow("mask",mask);
 GpuMat gpuMat,output,mask_gpu,dst,dst_mask;
 gpuMat.upload(image);
 mask_gpu.upload(mask);
 AddColor(gpuMat,mask_gpu,dst,dst_mask);
 namedWindow("1",CV_WINDOW_OPENGL);
 imshow("1",dst);
 waitKey(0);
 return 0;
}

  
}

a weird wierd result of a project with GpuMat and cuda

The code like following 

#include <opencv2/core/core.hpp>
 #include <opencv2/gpu/gpu.hpp>
 #include <opencv2/core/cuda_devptrs.hpp>
 #include <opencv2/gpu/stream_accessor.hpp>
 #include <opencv2/gpu/device/common.hpp>  
 #include <opencv2/highgui/highgui.hpp>
 #include <iostream>
 #include <cuda_runtime.h>
 using namespace std;
 using namespace cv;
 using namespace cv::gpu;

cv::gpu;  
    __global__ void AddColor_Kernel(const PtrStepSz<uchar3> src,const PtrStepSz<uchar> mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask)
 {
    int x = blockIdx.x * blockDim.x + threadIdx.x;
    int y = blockIdx.y * blockDim.y + threadIdx.x;

    if(y < mask.rows && x < mask.cols)
    {
        if(mask(y,x))
            dst.ptr(y )[ x] = src.ptr(y)[x];
        dst_mask.ptr(y )[ x] |= mask.ptr(y)[x];
    }
}




 void AddColorCaller(const PtrStepSz<uchar3> &src,const PtrStepSz<uchar> &mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask,cudaStream_t stream)
 {

    dim3 block(32,8);
    //  dim3 grid(divUp(src.cols ,block.x),divUp(src.rows ,block.y));
    dim3 grid((mask.cols + block.x - 1)/block.x,(mask.rows + block.y - 1)/block.y);
    AddColor_Kernel<<<grid,block,0,stream>>>(src,mask,dst,dst_mask);
    cudaSafeCall(cudaGetLastError());
    if(stream == 0)
        cudaSafeCall(cudaDeviceSynchronize());
}

void AddColor(const GpuMat &src,const GpuMat &mask,  GpuMat &dst,  GpuMat &dst_mask,Stream& stream = Stream::Null())
{   
    dst.create(src.size(),src.type());
    dst.setTo(Scalar::all(0));
    dst_mask.create(mask.size(),mask.type());
    dst_mask.setTo(Scalar::all(0));
    cudaStream_t st = StreamAccessor::getStream(stream);
    AddColorCaller(src,mask,dst,dst_mask,st);
}

int main()
{
    Mat image = imread("1.jpg");
    Mat mask  = imread("mask.jpg",-1);
    cout<<mask.channels()<<endl;
    resize(mask,mask,image.size());

    imshow("src",image);
    imshow("mask",mask);
    GpuMat gpuMat,output,mask_gpu,dst,dst_mask;

    gpuMat.upload(image);
    mask_gpu.upload(mask);
    AddColor(gpuMat,mask_gpu,dst,dst_mask);
    namedWindow("1",CV_WINDOW_OPENGL);
    imshow("1",dst);
    waitKey(0); 
    return 0;
}

a wierd result of a project with GpuMat and cuda

The code like following 

#include <opencv2/core/core.hpp>
 #include <opencv2/gpu/gpu.hpp>
 #include <opencv2/core/cuda_devptrs.hpp>
 #include <opencv2/gpu/stream_accessor.hpp>
 #include <opencv2/gpu/device/common.hpp>  
 #include <opencv2/highgui/highgui.hpp>
 #include <iostream>
 #include <cuda_runtime.h>
 using namespace std;
 using namespace cv;
 using namespace cv::gpu;  
    cv::gpu;

__global__ void AddColor_Kernel(const PtrStepSz<uchar3> src,const PtrStepSz<uchar> mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask)
 {
    int x = blockIdx.x * blockDim.x + threadIdx.x;
    int y = blockIdx.y * blockDim.y + threadIdx.x;

    if(y < mask.rows && x < mask.cols)
    {
        if(mask(y,x))
            dst.ptr(y )[ x] = src.ptr(y)[x];
        dst_mask.ptr(y )[ x] |= mask.ptr(y)[x];
    }
}




 void AddColorCaller(const PtrStepSz<uchar3> &src,const PtrStepSz<uchar> &mask, PtrStep<uchar3> dst, PtrStep<uchar> dst_mask,cudaStream_t stream)
 {

    dim3 block(32,8);
    //  dim3 grid(divUp(src.cols ,block.x),divUp(src.rows ,block.y));
    dim3 grid((mask.cols + block.x - 1)/block.x,(mask.rows + block.y - 1)/block.y);
    AddColor_Kernel<<<grid,block,0,stream>>>(src,mask,dst,dst_mask);
    cudaSafeCall(cudaGetLastError());
    if(stream == 0)
        cudaSafeCall(cudaDeviceSynchronize());
}

void AddColor(const GpuMat &src,const GpuMat &mask,  GpuMat &dst,  GpuMat &dst_mask,Stream& stream = Stream::Null())
{   
    dst.create(src.size(),src.type());
    dst.setTo(Scalar::all(0));
    dst_mask.create(mask.size(),mask.type());
    dst_mask.setTo(Scalar::all(0));
    cudaStream_t st = StreamAccessor::getStream(stream);
    AddColorCaller(src,mask,dst,dst_mask,st);
}

int main()
{
    Mat image = imread("1.jpg");
    Mat mask  = imread("mask.jpg",-1);
    cout<<mask.channels()<<endl;
    resize(mask,mask,image.size());

    imshow("src",image);
    imshow("mask",mask);
    GpuMat gpuMat,output,mask_gpu,dst,dst_mask;

    gpuMat.upload(image);
    mask_gpu.upload(mask);
    AddColor(gpuMat,mask_gpu,dst,dst_mask);
    namedWindow("1",CV_WINDOW_OPENGL);
    imshow("1",dst);
    waitKey(0); 
    return 0;
}

origin_mask processed_final_mask image description

According to code,the final_mask should be the same as origin_mask.The pic should be cut according to the mask.But result is disappointed,So I hope somebody can point out error of my code.Thanks!

a wierd result of a project with GpuMat and cuda

The code like following 

#include <opencv2/core/core.hpp>
#include <opencv2/gpu/gpu.hpp>
#include <opencv2/core/cuda_devptrs.hpp>
#include <opencv2/gpu/stream_accessor.hpp>
#include <opencv2/gpu/device/common.hpp>  
#include <opencv2/highgui/highgui.hpp>
#include <iostream>
#include <cuda_runtime.h>
using namespace std;
using namespace cv;
using namespace cv::gpu;

__global__ void AddColor_Kernel(const PtrStepSz<uchar3> src,const PtrStepSz<uchar> mask,  PtrStep<uchar3> dst, PtrStep<uchar> dst_mask)
{
    int x = blockIdx.x * blockDim.x + threadIdx.x;
    int y = blockIdx.y * blockDim.y + threadIdx.x;

    if(y < mask.rows && x < mask.cols)
    {
        if(mask(y,x))
            dst.ptr(y )[ x] = src.ptr(y)[x];
        dst_mask.ptr(y )[ x] |= mask.ptr(y)[x];
    }
}




void AddColorCaller(const PtrStepSz<uchar3> &src,const PtrStepSz<uchar> &mask, PtrStep<uchar3> dst, dst,
PtrStep<uchar> dst_mask,cudaStream_t stream)
 {

    dim3 block(32,8);
    //  dim3 grid(divUp(src.cols ,block.x),divUp(src.rows ,block.y));
    dim3 grid((mask.cols + block.x - 1)/block.x,(mask.rows + block.y - 1)/block.y);
    AddColor_Kernel<<<grid,block,0,stream>>>(src,mask,dst,dst_mask);
    cudaSafeCall(cudaGetLastError());
    if(stream == 0)
        cudaSafeCall(cudaDeviceSynchronize());
}

void AddColor(const GpuMat &src,const GpuMat &mask,  GpuMat &dst,  GpuMat &dst_mask,Stream& &dst_mask,
Stream& stream = Stream::Null())
 {   
     dst.create(src.size(),src.type());
     dst.setTo(Scalar::all(0));
     dst_mask.create(mask.size(),mask.type());
     dst_mask.setTo(Scalar::all(0));
     cudaStream_t st = StreamAccessor::getStream(stream);
     AddColorCaller(src,mask,dst,dst_mask,st);
 }

int main()
{
    Mat image = imread("1.jpg");
    Mat mask  = imread("mask.jpg",-1);
    cout<<mask.channels()<<endl;
    resize(mask,mask,image.size());

    imshow("src",image);
    imshow("mask",mask);
    GpuMat gpuMat,output,mask_gpu,dst,dst_mask;

    gpuMat.upload(image);
    mask_gpu.upload(mask);
    AddColor(gpuMat,mask_gpu,dst,dst_mask);
    namedWindow("1",CV_WINDOW_OPENGL);
    imshow("1",dst);
    waitKey(0); 
    return 0;
}

origin_mask processed_final_mask image description

According to code,the final_mask should be the same as origin_mask.The pic should be cut according to the mask.But result is disappointed,So I hope somebody can point out error of my code.Thanks!

Copyright OpenCV foundation, 2012-2018. Content on this site is licensed under a Creative Commons Attribution Share Alike 3.0 license.
about | faq | help | privacy policy | terms of service
Powered by Askbot version 0.10.2