Skip to content
New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Adding headers to projects and applied clang-tidy #171

Merged
merged 4 commits into from
May 14, 2020
Merged
Show file tree
Hide file tree
Changes from 2 commits
Commits
File filter

Filter by extension

Filter by extension

Conversations
Failed to load comments.
Loading
Jump to
Jump to file
Failed to load files.
Loading
Diff view
Diff view
3 changes: 3 additions & 0 deletions .clang-tidy
Original file line number Diff line number Diff line change
@@ -0,0 +1,3 @@
---
Checks: '*,-llvm-header-guard,-fuchsia-default-arguments-declarations,-cppcoreguidelines-no-malloc,-cppcoreguidelines-owning-memory,-modernize-use-trailing-return-type,-misc-non-private-member-variables-in-classes'
HeaderFilterRegex: '.*'
11 changes: 7 additions & 4 deletions CMakeLists.txt
Original file line number Diff line number Diff line change
Expand Up @@ -30,7 +30,6 @@ if(NOT DEFINED COMPUTE_CAPABILITY)
set(COMPUTE_CAPABILITY "30")
endif()
set(CMAKE_CUDA_FLAGS "${CMAKE_CUDA_FLAGS} -arch=sm_${COMPUTE_CAPABILITY} -use_fast_math")
include_directories(${CMAKE_CURRENT_SOURCE_DIR})

OPTION(CUDA_OUTPUT_INTERMEDIATE_CODE "Output ptx code" OFF)
if(CUDA_OUTPUT_INTERMEDIATE_CODE)
Expand Down Expand Up @@ -72,9 +71,13 @@ INSTALL(
###############################################################################
# Executables
###############################################################################
add_custom_target(examples DEPENDS mallocMC_Example01 mallocMC_Example02 mallocMC_Example03 VerifyHeap)
file(GLOB_RECURSE headers src/include/**)
add_custom_target(mallocMC SOURCES ${headers}) # create a target with the header files for IDE projects
source_group(TREE ${CMAKE_CURRENT_LIST_DIR}/src/include FILES ${headers})

add_executable(mallocMC_Example01 EXCLUDE_FROM_ALL examples/mallocMC_example01.cu)
include_directories(${CMAKE_CURRENT_LIST_DIR}/src/include)
add_executable(mallocMC_Example01 EXCLUDE_FROM_ALL examples/mallocMC_example01.cu examples/mallocMC_example01_config.hpp)
bernhardmgruber marked this conversation as resolved.
Show resolved Hide resolved
add_executable(mallocMC_Example02 EXCLUDE_FROM_ALL examples/mallocMC_example02.cu)
add_executable(mallocMC_Example03 EXCLUDE_FROM_ALL examples/mallocMC_example03.cu)
add_executable(VerifyHeap EXCLUDE_FROM_ALL tests/verify_heap.cu)
add_executable(VerifyHeap EXCLUDE_FROM_ALL tests/verify_heap.cu tests/verify_heap_config.hpp)
add_custom_target(examples DEPENDS mallocMC_Example01 mallocMC_Example02 mallocMC_Example03 VerifyHeap)
2 changes: 1 addition & 1 deletion examples/mallocMC_example01.cu
Original file line number Diff line number Diff line change
Expand Up @@ -32,7 +32,7 @@
#include <numeric>

#include <cuda.h>
#include "mallocMC_example01_config.cu"
#include "mallocMC_example01_config.hpp"

void run();

Expand Down
Original file line number Diff line number Diff line change
Expand Up @@ -29,14 +29,14 @@
#pragma once

// basic files for mallocMC
#include "src/include/mallocMC/mallocMC_hostclass.hpp"
#include <mallocMC/mallocMC_hostclass.hpp>

// Load all available policies for mallocMC
#include "src/include/mallocMC/CreationPolicies.hpp"
#include "src/include/mallocMC/DistributionPolicies.hpp"
#include "src/include/mallocMC/OOMPolicies.hpp"
#include "src/include/mallocMC/ReservePoolPolicies.hpp"
#include "src/include/mallocMC/AlignmentPolicies.hpp"
#include <mallocMC/CreationPolicies.hpp>
#include <mallocMC/DistributionPolicies.hpp>
#include <mallocMC/OOMPolicies.hpp>
#include <mallocMC/ReservePoolPolicies.hpp>
#include <mallocMC/AlignmentPolicies.hpp>

// configurate the CreationPolicy "Scatter" to modify the default behaviour
struct ScatterHeapConfig : mallocMC::CreationPolicies::Scatter<>::HeapProperties{
Expand Down
12 changes: 6 additions & 6 deletions examples/mallocMC_example02.cu
Original file line number Diff line number Diff line change
Expand Up @@ -37,14 +37,14 @@
// includes for mallocMC
///////////////////////////////////////////////////////////////////////////////
// basic files for mallocMC
#include "src/include/mallocMC/mallocMC_hostclass.hpp"
#include <mallocMC/mallocMC_hostclass.hpp>

// Load all available policies for mallocMC
#include "src/include/mallocMC/CreationPolicies.hpp"
#include "src/include/mallocMC/DistributionPolicies.hpp"
#include "src/include/mallocMC/OOMPolicies.hpp"
#include "src/include/mallocMC/ReservePoolPolicies.hpp"
#include "src/include/mallocMC/AlignmentPolicies.hpp"
#include <mallocMC/CreationPolicies.hpp>
#include <mallocMC/DistributionPolicies.hpp>
#include <mallocMC/OOMPolicies.hpp>
#include <mallocMC/ReservePoolPolicies.hpp>
#include <mallocMC/AlignmentPolicies.hpp>

///////////////////////////////////////////////////////////////////////////////
// Configuration for mallocMC
Expand Down
14 changes: 6 additions & 8 deletions examples/mallocMC_example03.cu
Original file line number Diff line number Diff line change
Expand Up @@ -38,14 +38,12 @@
///////////////////////////////////////////////////////////////////////////////
// includes for mallocMC
///////////////////////////////////////////////////////////////////////////////
#include "src/include/mallocMC/mallocMC_hostclass.hpp"

#include "src/include/mallocMC/CreationPolicies.hpp"
#include "src/include/mallocMC/DistributionPolicies.hpp"
#include "src/include/mallocMC/OOMPolicies.hpp"
#include "src/include/mallocMC/ReservePoolPolicies.hpp"
#include "src/include/mallocMC/AlignmentPolicies.hpp"

#include <mallocMC/mallocMC_hostclass.hpp>
#include <mallocMC/CreationPolicies.hpp>
#include <mallocMC/DistributionPolicies.hpp>
#include <mallocMC/OOMPolicies.hpp>
#include <mallocMC/ReservePoolPolicies.hpp>
#include <mallocMC/AlignmentPolicies.hpp>

///////////////////////////////////////////////////////////////////////////////
// Configuration for mallocMC
Expand Down
2 changes: 1 addition & 1 deletion src/include/mallocMC/alignmentPolicies/Noop_impl.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -31,8 +31,8 @@
#include <string>
#include <tuple>

#include "Noop.hpp"
#include "../mallocMC_prefixes.hpp"
#include "Noop.hpp"

namespace mallocMC{
namespace AlignmentPolicies{
Expand Down
2 changes: 1 addition & 1 deletion src/include/mallocMC/alignmentPolicies/Shrink.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -38,7 +38,7 @@ namespace ShrinkConfig{
struct DefaultShrinkConfig{
static constexpr auto dataAlignment = 16;
};
}
} // namespace ShrinkConfig

/**
* @brief Provides proper alignment of pool and pads memory requests
Expand Down
14 changes: 7 additions & 7 deletions src/include/mallocMC/alignmentPolicies/Shrink_impl.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -33,11 +33,11 @@

#include <cstdint>
#include <iostream>
#include <string>
#include <sstream>
#include <string>

#include "Shrink.hpp"
#include "../mallocMC_prefixes.hpp"
#include "Shrink.hpp"

namespace mallocMC{
namespace AlignmentPolicies{
Expand All @@ -46,17 +46,17 @@ namespace Shrink2NS{

template<int PSIZE> struct __PointerEquivalent{ typedef unsigned int type;};
template<>
struct __PointerEquivalent<8>{ typedef unsigned long long int type; };
}// namespace ShrinkNS
struct __PointerEquivalent<8>{ using type = unsigned long long; };
} // namespace Shrink2NS

template<typename T_Config>
class Shrink{
public:
typedef T_Config Properties;
using Properties = T_Config;

private:
using uint32 = std::uint32_t;
typedef Shrink2NS::__PointerEquivalent<sizeof(char*)>::type PointerEquivalent;
using PointerEquivalent = Shrink2NS::__PointerEquivalent<sizeof(char*)>::type;

/** Allow for a hierarchical validation of parameters:
*
Expand All @@ -73,7 +73,7 @@ namespace Shrink2NS{
static constexpr uint32 dataAlignment = MALLOCMC_AP_SHRINK_DATAALIGNMENT;

//dataAlignment must be a power of 2!
static_assert(dataAlignment && !(dataAlignment & (dataAlignment-1)), "dataAlignment must also be a power of 2");
static_assert(dataAlignment != 0 && (dataAlignment & (dataAlignment-1)) == 0, "dataAlignment must also be a power of 2");

public:
static std::tuple<void*,size_t> alignPool(void* memory, size_t memsize){
Expand Down
26 changes: 13 additions & 13 deletions src/include/mallocMC/allocator.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -28,15 +28,16 @@

#pragma once

#include "mallocMC_utils.hpp"
#include "device_allocator.hpp"
#include "mallocMC_allocator_handle.hpp"
#include "mallocMC_constraints.hpp"
#include "mallocMC_prefixes.hpp"
#include "mallocMC_traits.hpp"
#include "mallocMC_allocator_handle.hpp"
#include "mallocMC_utils.hpp"

#include <cstdint>
#include <tuple>
#include <sstream>
#include <tuple>
#include <vector>

namespace mallocMC{
Expand Down Expand Up @@ -71,7 +72,7 @@ namespace detail{
return T_Allocator::CreationPolicy::getAvailableSlotsHost(slotSize, alloc.getAllocatorHandle().devAllocator);
}
};
}
} // namespace detail

struct HeapInfo
{
Expand Down Expand Up @@ -113,18 +114,17 @@ namespace detail{

public:
typedef T_CreationPolicy CreationPolicy;
typedef T_DistributionPolicy DistributionPolicy;
typedef T_OOMPolicy OOMPolicy;
typedef T_ReservePoolPolicy ReservePoolPolicy;
typedef T_AlignmentPolicy AlignmentPolicy;
typedef std::vector< HeapInfo > HeapInfoVector;
typedef DeviceAllocator<
using DistributionPolicy = T_DistributionPolicy;
using OOMPolicy = T_OOMPolicy;
using ReservePoolPolicy = T_ReservePoolPolicy;
using AlignmentPolicy = T_AlignmentPolicy;
using HeapInfoVector = std::vector<HeapInfo>;
using DevAllocator = DeviceAllocator<
CreationPolicy,
DistributionPolicy,
OOMPolicy,
AlignmentPolicy
> DevAllocator;
typedef AllocatorHandleImpl<Allocator> AllocatorHandle;
AlignmentPolicy>;
using AllocatorHandle = AllocatorHandleImpl<Allocator>;

private:
AllocatorHandle allocatorHandle;
Expand Down
2 changes: 1 addition & 1 deletion src/include/mallocMC/creationPolicies/OldMalloc_impl.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -52,7 +52,7 @@ namespace CreationPolicies{
}

__device__ bool isOOM(void* p, size_t s) const {
return s && (p == nullptr);
return s != 0 && (p == nullptr);
}

template < typename T >
Expand Down
2 changes: 1 addition & 1 deletion src/include/mallocMC/creationPolicies/Scatter.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -50,7 +50,7 @@ namespace ScatterConf{
static constexpr auto hashingDistWP = 1;
static constexpr auto hashingDistWPRel = 1;
};
}
} // namespace ScatterConf

/**
* @brief fast memory allocation based on ScatterAlloc
Expand Down
8 changes: 4 additions & 4 deletions src/include/mallocMC/creationPolicies/Scatter_impl.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -33,12 +33,12 @@

#pragma once

#include <cstdio>
#include <cassert>
#include <cstdint> /* uint32_t */
#include <cstdio>
#include <iostream>
#include <string>
#include <cassert>
#include <stdexcept>
#include <string>

#include "../mallocMC_utils.hpp"
#include "Scatter.hpp"
Expand Down Expand Up @@ -75,7 +75,7 @@ namespace ScatterKernelDetail{
{
public:
typedef T_Config HeapProperties;
bernhardmgruber marked this conversation as resolved.
Show resolved Hide resolved
typedef T_Hashing HashingProperties;
using HashingProperties = T_Hashing;
struct Properties : HeapProperties, HashingProperties{};
static constexpr auto providesAvailableSlots = true;

Expand Down
10 changes: 5 additions & 5 deletions src/include/mallocMC/device_allocator.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -28,10 +28,10 @@

#pragma once

#include "mallocMC_utils.hpp"
#include "mallocMC_constraints.hpp"
#include "mallocMC_prefixes.hpp"
#include "mallocMC_traits.hpp"
#include "mallocMC_utils.hpp"

#include <cstdint>
#include <cstdio>
Expand Down Expand Up @@ -114,10 +114,10 @@ namespace detail{
{
using uint32 = std::uint32_t;
public:
typedef T_CreationPolicy CreationPolicy;
typedef T_DistributionPolicy DistributionPolicy;
typedef T_OOMPolicy OOMPolicy;
typedef T_AlignmentPolicy AlignmentPolicy;
using CreationPolicy = T_CreationPolicy;
using DistributionPolicy = T_DistributionPolicy;
using OOMPolicy = T_OOMPolicy;
using AlignmentPolicy = T_AlignmentPolicy;

void* pool;

Expand Down
2 changes: 1 addition & 1 deletion src/include/mallocMC/distributionPolicies/Noop_impl.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -30,8 +30,8 @@
#include <cstdint>
#include <string>

#include "Noop.hpp"
#include "../mallocMC_prefixes.hpp"
#include "Noop.hpp"

namespace mallocMC{
namespace DistributionPolicies{
Expand Down
2 changes: 1 addition & 1 deletion src/include/mallocMC/distributionPolicies/XMallocSIMD.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -40,7 +40,7 @@ namespace DistributionPolicies{
struct DefaultXMallocConfig{
static constexpr auto pagesize = 4096;
};
}
} // namespace XMallocSIMDConf

/**
* @brief SIMD optimized chunk resizing in the style of XMalloc
Expand Down
Original file line number Diff line number Diff line change
Expand Up @@ -35,11 +35,11 @@

#include <cstdint>
#include <limits>
#include <string>
#include <sstream>
#include <string>

#include "../mallocMC_utils.hpp"
#include "../mallocMC_prefixes.hpp"
#include "../mallocMC_utils.hpp"
#include "XMallocSIMD.hpp"

namespace mallocMC{
Expand All @@ -57,7 +57,7 @@ namespace DistributionPolicies{
uint32 threadcount;
uint32 req_size;
public:
typedef T_Config Properties;
using Properties = T_Config;

MAMC_ACCELERATOR
XMallocSIMD() : can_use_coalescing(false), warpid(warpid_withinblock()),
Expand Down
4 changes: 2 additions & 2 deletions src/include/mallocMC/mallocMC.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -43,8 +43,8 @@
#include "mallocMC_hostclass.hpp"

// all the policies
#include "AlignmentPolicies.hpp"
#include "CreationPolicies.hpp"
#include "DistributionPolicies.hpp"
#include "ReservePoolPolicies.hpp"
#include "AlignmentPolicies.hpp"
#include "OOMPolicies.hpp"
#include "ReservePoolPolicies.hpp"
4 changes: 2 additions & 2 deletions src/include/mallocMC/mallocMC_allocator_handle.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -35,11 +35,11 @@ namespace mallocMC{
template <typename T_HostAllocator>
struct AllocatorHandleImpl
{
typedef typename T_HostAllocator::DevAllocator DevAllocator;
using DevAllocator = typename T_HostAllocator::DevAllocator;

DevAllocator* devAllocator;

AllocatorHandleImpl(
explicit AllocatorHandleImpl(
DevAllocator* p
) :
devAllocator( p )
Expand Down
4 changes: 2 additions & 2 deletions src/include/mallocMC/mallocMC_hostclass.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -28,6 +28,6 @@

#pragma once

#include "mallocMC_traits.hpp"
#include "device_allocator.hpp"
#include "allocator.hpp"
#include "device_allocator.hpp"
#include "mallocMC_traits.hpp"
2 changes: 2 additions & 0 deletions src/include/mallocMC/mallocMC_prefixes.hpp
Original file line number Diff line number Diff line change
Expand Up @@ -28,6 +28,8 @@

#pragma once

#include <device_launch_parameters.h>

#define MAMC_HOST __host__
#define MAMC_ACCELERATOR __device__

Loading