mirror of
https://github.com/facebookresearch/faiss.git
synced 2025-06-03 21:54:02 +08:00
784e2facd8
* moved most FAISS_ASSERT calls to C++ exceptions, and adjusted memory allocation to avoid mem leaks * added an IndexIVFScalarQuantizer type that offers an intermediate compression between IVFFlat and IVFPQ * support removal of indices in IndexIDMap / IndexFlat combination * various fixes in GPU code
34 lines
937 B
C++
34 lines
937 B
C++
/**
|
|
* Copyright (c) 2015-present, Facebook, Inc.
|
|
* All rights reserved.
|
|
*
|
|
* This source code is licensed under the CC-by-NC license found in the
|
|
* LICENSE file in the root directory of this source tree.
|
|
*/
|
|
|
|
// Copyright 2004-present Facebook. All Rights Reserved.
|
|
|
|
#include "MemorySpace.h"
|
|
#include <cuda_runtime.h>
|
|
|
|
namespace faiss { namespace gpu {
|
|
|
|
/// Allocates CUDA memory for a given memory space
|
|
void allocMemorySpace(MemorySpace space, void** p, size_t size) {
|
|
if (space == MemorySpace::Device) {
|
|
FAISS_ASSERT_FMT(cudaMalloc(p, size) == cudaSuccess,
|
|
"Failed to cudaMalloc %zu bytes", size);
|
|
}
|
|
#ifdef FAISS_UNIFIED_MEM
|
|
else if (space == MemorySpace::Unified) {
|
|
FAISS_ASSERT_FMT(cudaMallocManaged(p, size) == cudaSuccess,
|
|
"Failed to cudaMallocManaged %zu bytes", size);
|
|
}
|
|
#endif
|
|
else {
|
|
FAISS_ASSERT_FMT(false, "Unknown MemorySpace %d", (int) space);
|
|
}
|
|
}
|
|
|
|
} }
|