Add property_list to alloc func. Fix alignment and size param order.

Author: przemektmalon

sycl/doc/extensions/experimental/sycl_ext_oneapi_memory_export.asciidoc

@@ -161,14 +161,16 @@ the exported memory handle based on the `export_external_mem_handle_type`.
 namespace sycl::ext::oneapi::experimental {
 
 void *alloc_exportable_device_mem(
-    size_t size, size_t alignment,
+    size_t alignment, size_t size,
     export_external_mem_handle_type exportMemHandleType,
-    const sycl::device &syclDevice, const sycl::context &syclContext);
+    const sycl::device &syclDevice, const sycl::context &syclContext,
+    const property_list& propList = {});
 
 void *alloc_exportable_device_mem(
-    size_t size, size_t alignment,
+    size_t alignment, size_t size,
     export_external_mem_handle_type exportMemHandleType,
-    const sycl::queue &syclQueue);
+    const sycl::queue &syclQueue,
+    const property_list& propList = {});
 }
 ```
 
@@ -190,6 +192,11 @@ Memory allocated through this function has a linear memory layout on the device
 (which is the same as memory allocated by other USM allocation functions like 
 `sycl::malloc_device`).
 
+Zero or more properties can be passed in the `propList` parameter via an
+instance of `sycl::property_list`. Currently, this extension does not define
+any properties that can be used with this function, so the `propList` parameter
+is ignored and reserved for future use.
+
 If an invalid `exportMemHandleType` is passed, the function will throw a
 `sycl::exception` with the `errc::invalid` code.
 

sycl/include/sycl/ext/oneapi/memory_export.hpp

@@ -53,15 +53,16 @@ export_device_mem_win32_nt(void *deviceMemory, const sycl::device &syclDevice,
 __SYCL_EXPORT void *alloc_exportable_device_mem(
     size_t alignment, size_t size,
     export_external_mem_handle_type externalMemHandleType,
-    const sycl::device &syclDevice, const sycl::context &syclContext);
+    const sycl::device &syclDevice, const sycl::context &syclContext,
+    const sycl::property_list &propList = {});
 
 inline void *alloc_exportable_device_mem(
     size_t alignment, size_t size,
     export_external_mem_handle_type externalMemHandleType,
-    const sycl::queue &syclQueue) {
-  return alloc_exportable_device_mem(size, alignment, externalMemHandleType,
+    const sycl::queue &syclQueue, const sycl::property_list &propList = {}) {
+  return alloc_exportable_device_mem(alignment, size, externalMemHandleType,
                                      syclQueue.get_device(),
-                                     syclQueue.get_context());
+                                     syclQueue.get_context(), propList);
 }
 
 __SYCL_EXPORT void free_exportable_memory(void *deviceMemory,

sycl/source/detail/memory_export.cpp

@@ -23,7 +23,8 @@ namespace ext::oneapi::experimental {
 __SYCL_EXPORT void *alloc_exportable_device_mem(
     size_t alignment, size_t size,
     export_external_mem_handle_type externalMemHandleType,
-    const sycl::device &syclDevice, const sycl::context &syclContext) {
+    const sycl::device &syclDevice, const sycl::context &syclContext,
+    const sycl::property_list& propList) {
 
   if (!syclDevice.has(sycl::aspect::ext_oneapi_memory_export_linear)) {
     throw sycl::exception(

sycl/test-e2e/MemoryExport/export_memory_api_test.cpp

@@ -36,8 +36,8 @@ int main() {
   try {
     // Allocate exportable memory.
     size_t size = 1024;
-    void *mem = syclexp::alloc_exportable_device_mem(0, size, exportHandleType,
-                                                     device, context);
+    void *mem = syclexp::alloc_exportable_device_mem(
+        0 /* alignment */, size, exportHandleType, device, context);
 
     // Export the memory handle.
     syclexp::exported_mem_t<exportHandleType> exportableMemoryHandle =