… | |
… | |
100 | #define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore") |
100 | #define ECB_MEMORY_FENCE_RELEASE __asm__ __volatile__ ("membar #LoadStore | #StoreStore") |
101 | #elif defined(__s390__) || defined(__s390x__) |
101 | #elif defined(__s390__) || defined(__s390x__) |
102 | #define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory") |
102 | #define ECB_MEMORY_FENCE __asm__ __volatile__ ("bcr 15,0" : : : "memory") |
103 | #elif defined(__mips__) |
103 | #elif defined(__mips__) |
104 | #define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory") |
104 | #define ECB_MEMORY_FENCE __asm__ __volatile__ ("sync" : : : "memory") |
105 | #elif __xlC__ |
|
|
106 | #define ECB_MEMORY_FENCE __lwsync () |
|
|
107 | #endif |
105 | #endif |
108 | #endif |
106 | #endif |
109 | #endif |
107 | #endif |
110 | |
108 | |
111 | #ifndef ECB_MEMORY_FENCE |
109 | #ifndef ECB_MEMORY_FENCE |
… | |
… | |
124 | #elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110 |
122 | #elif __SUNPRO_C >= 0x5110 || __SUNPRO_CC >= 0x5110 |
125 | #include <mbarrier.h> |
123 | #include <mbarrier.h> |
126 | #define ECB_MEMORY_FENCE __machine_rw_barrier () |
124 | #define ECB_MEMORY_FENCE __machine_rw_barrier () |
127 | #define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier () |
125 | #define ECB_MEMORY_FENCE_ACQUIRE __machine_r_barrier () |
128 | #define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier () |
126 | #define ECB_MEMORY_FENCE_RELEASE __machine_w_barrier () |
|
|
127 | #elif __xlC__ |
|
|
128 | #define ECB_MEMORY_FENCE __lwsync () |
129 | #endif |
129 | #endif |
130 | #endif |
130 | #endif |
131 | |
131 | |
132 | #ifndef ECB_MEMORY_FENCE |
132 | #ifndef ECB_MEMORY_FENCE |
133 | #if !ECB_AVOID_PTHREADS |
133 | #if !ECB_AVOID_PTHREADS |