TAPsCUDA_VertexList_Def.cu

Go to the documentation of this file.

/******************************************************************************
TAPsCUDA_VertexList_Def.cu

CUDA Vertex List Definition (i.e., cpp file).

SUKITTI PUNAK   (08/27/2008)
UPDATE          (09/17/2009)
******************************************************************************/

#include "TAPsCUDA_VertexList.cu"

BEGIN_NAMESPACE_TAPs__CUDA
//=============================================================================
//-----------------------------------------------------------------------------

//=============================================================================

// Constructor
DATA_Vertex_List::DATA_Vertex_List ( 
    unsigned int numOfVertices,         
    bool bIncludeHomeVertices,          
    unsigned int maxVextexConnection,   
    bool bIncludeSimFlagsConstraint,    
    bool bIncludeOrientations,          
    bool bIncludePrevOrientations,      
    bool bIncludeForces_1,              
    bool bIncludeForces_2               
) : 
    m_Ptr_Mem_VertexList( NULL ),
    m_Ptr_Mem_PrevVertexList( NULL ),
    m_Ptr_Mem_HomeVertexList( NULL ),
    m_Ptr_Mem_VertexConnectionList( NULL ),
    m_Ptr_Mem_OrientationList( NULL ),
    m_Ptr_Mem_PrevOrientationList( NULL ),
    m_Ptr_Mem_ForceList_1( NULL ),
    m_Ptr_Mem_ForceList_2( NULL ),
    
    m_Ptr_Mem_SimFlagsList( NULL ),
    m_Ptr_Mem_PosConstraintList( NULL ),
    
    m_uiNumOfVertices( numOfVertices ), 
    m_bIncludeHomeVertices( bIncludeHomeVertices ), 
    m_uiMaxConnectionSize( maxVextexConnection ), 
    m_bIncludeSimFlagsConstraint( bIncludeSimFlagsConstraint ),
    m_bIncludeOrientations( bIncludeOrientations ),
    m_bIncludePrevOrientations( bIncludePrevOrientations ),
    m_bIncludeForces_1( bIncludeForces_1 ),
    m_bIncludeForces_2( bIncludeForces_2 )
{
    AllocateTextures();
}


// Destructor
DATA_Vertex_List::~DATA_Vertex_List ()
{
    DeallocateTextures();
    
}


// Allocate Textures
#ifdef  TAPs_CUDA_DATA_VERTEX_LIST_TEXTURE_FROM_LIN_MEM
bool DATA_Vertex_List::AllocateTextures ()
{
    //USE: cudaError_t cudaMalloc( void** devPtr, size_t count )

    if ( m_uiNumOfVertices > 0 ) {
        // Vertices
        CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_VertexList, m_uiNumOfVertices*4*sizeof(float) ) );
        CUT_CHECK_ERROR( "cudaMalloc for Vertex List Failed!" );
        // Previous vertices for the Verlet Integration
        CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_PrevVertexList, m_uiNumOfVertices*4*sizeof(float) ) );
        CUT_CHECK_ERROR( "cudaMalloc for Previous Vertex List Failed!" );
        // Home Vertices
        if ( m_bIncludeHomeVertices ) {
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_HomeVertexList, m_uiNumOfVertices*4*sizeof(float) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Home Vertex List Failed!" );
        }
        if ( m_uiMaxConnectionSize > 0 ) {
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_VertexConnectionList, m_uiNumOfVertices*m_uiMaxConnectionSize*sizeof(int) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Vertex Connection List Failed!" );
        }
        if ( m_bIncludeSimFlagsConstraint ) {
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_SimFlagsList, m_uiNumOfVertices*sizeof(unsigned int) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Simulation Flags List Failed!" );
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_PosConstraintList, m_uiNumOfVertices*4*sizeof(float) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Position Constraint List Failed!" );
        }
        if ( m_bIncludeOrientations ) {
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_OrientationList, m_uiNumOfVertices*4*sizeof(float) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Orientation List Failed!" );
        }
        if ( m_bIncludePrevOrientations ) {
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_PrevOrientationList, m_uiNumOfVertices*4*sizeof(float) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Previous Orientation List Failed!" );
        }
        if ( m_bIncludeForces_1 ) {
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_ForceList_1, m_uiNumOfVertices*4*sizeof(float) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Force List Set 1 Failed!" );
        }
        if ( m_bIncludeForces_2 ) {
            CUDA_SAFE_CALL( cudaMalloc( (void**)&m_Ptr_Mem_ForceList_2, m_uiNumOfVertices*4*sizeof(float) ) );
            CUT_CHECK_ERROR( "cudaMalloc for Force List Set 2 Failed!" );
        }
    }
    return true;
}
#endif//TAPs_CUDA_DATA_VERTEX_LIST_TEXTURE_FROM_LIN_MEM


// Deallocate Textures
#ifdef  TAPs_CUDA_DATA_VERTEX_LIST_TEXTURE_FROM_LIN_MEM
bool DATA_Vertex_List::DeallocateTextures ()
{
    //USE: cudaError_t cudaFree(void* devPtr)

    if ( m_uiNumOfVertices > 0 ) {
        CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_VertexList ) );
        m_Ptr_Mem_VertexList = NULL;
        CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_PrevVertexList ) );
        m_Ptr_Mem_PrevVertexList = NULL;
        if ( m_bIncludeHomeVertices ) {
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_HomeVertexList ) );
            m_Ptr_Mem_HomeVertexList = NULL;
        }
        if ( m_uiMaxConnectionSize > 0 ) {
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_VertexConnectionList ) );
            m_Ptr_Mem_VertexConnectionList = NULL;
        }
        if ( m_bIncludeSimFlagsConstraint ) {
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_SimFlagsList ) );
            m_Ptr_Mem_SimFlagsList = NULL;
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_PosConstraintList ) );
            m_Ptr_Mem_PosConstraintList = NULL;
        }
        if ( m_bIncludeOrientations ) {
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_OrientationList ) );
            m_Ptr_Mem_OrientationList = NULL;
        }
        if ( m_bIncludePrevOrientations ) {
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_PrevOrientationList ) );
            m_Ptr_Mem_PrevOrientationList = NULL;
        }
        if ( m_bIncludeForces_1 ) {
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_ForceList_1 ) );
            m_Ptr_Mem_ForceList_1 = NULL;
        }
        if ( m_bIncludeForces_2 ) {
            CUDA_SAFE_CALL( cudaFree( m_Ptr_Mem_ForceList_2 ) );
            m_Ptr_Mem_ForceList_2 = NULL;
        }
    }
    return true;
}
#endif//TAPs_CUDA_DATA_VERTEX_LIST_TEXTURE_FROM_LIN_MEM

// END: class DATA_Vertex_List
//=============================================================================

//-----------------------------------------------------------------------------
//=============================================================================
END_NAMESPACE_TAPs__CUDA
//-----------------------------------------------------------------------------
//34567890123456789012345678901234567890123456789012345678901234567890123456789
//--+----1----+----2----+----3----+----4----+----5----+----6----+----7----+----