/* -*- mode: c++; c-basic-offset: 4; tab-width: 4; indent-tabs-mode: t -*-
* vim: ts=4 sw=4 noet ai cindent syntax=cpp
*
* Conky, a system monitor, based on torsmo
*
* Any original torsmo code is licensed under the BSD license
*
* All code written since the fork of torsmo is licensed under the GPL
*
* Please see COPYING for details
*
* Copyright (c) 2004, Hannu Saransaari and Lauri Hakkarainen
* Copyright (c) 2005-2010 Brenden Matthews, Philip Kovacs, et. al.
* (see AUTHORS)
* All rights reserved.
*
* This program is free software: you can redistribute it and/or modify
* it under the terms of the GNU General Public License as published by
* the Free Software Foundation, either version 3 of the License, or
* (at your option) any later version.
*
* This program is distributed in the hope that it will be useful,
* but WITHOUT ANY WARRANTY; without even the implied warranty of
* MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the
* GNU General Public License for more details.
* You should have received a copy of the GNU General Public License
* along with this program. If not, see .
*
*/
#include "config.h"
#include "conky.h"
#include "fs.h"
#include "logging.h"
#include "net_stat.h"
#include "specials.h"
#include "temphelper.h"
#include "timeinfo.h"
#include "top.h"
#include
#include
#include
#include
#include
#include
#include
#include
#include
#include
#include
/* check for OS and include appropriate headers */
#if defined(__linux__)
#include "linux.h"
#elif defined(__FreeBSD__) || defined(__FreeBSD_kernel__)
#include "freebsd.h"
#elif defined(__OpenBSD__)
#include "openbsd.h"
#endif
/* folds a string over top of itself, like so:
*
* if start is "blah", and you call it with count = 1, the result will be "lah"
*/
void strfold(char *start, int count)
{
char *curplace;
for (curplace = start + count; *curplace != 0; curplace++) {
*(curplace - count) = *curplace;
}
*(curplace - count) = 0;
}
#ifndef HAVE_STRNDUP
// use our own strndup() if it's not available
char *strndup(const char *s, size_t n)
{
if (strlen(s) > n) {
char *ret = malloc(n + 1);
strncpy(ret, s, n);
ret[n] = 0;
return ret;
} else {
return strdup(s);
}
}
#endif /* HAVE_STRNDUP */
void update_uname(void)
{
uname(&info.uname_s);
}
double get_time(void)
{
struct timeval tv;
gettimeofday(&tv, 0);
return tv.tv_sec + (tv.tv_usec / 1000000.0);
}
/* Converts '~/...' paths to '/home/blah/...'
* It's similar to variable_substitute, except only cheques for $HOME and ~/ in path */
std::string to_real_path(const std::string &source)
{
const char *homedir = getenv("HOME");
if(source.find("~/") == 0)
return homedir + source.substr(1);
else if(source.find("$HOME/") == 0)
return homedir + source.substr(5);
else
return source;
}
int open_fifo(const char *file, int *reported)
{
int fd = 0;
fd = open(file, O_RDONLY | O_NONBLOCK);
if (fd == -1) {
if (!reported || *reported == 0) {
NORM_ERR("can't open %s: %s", file, strerror(errno));
if (reported) {
*reported = 1;
}
}
return -1;
}
return fd;
}
FILE *open_file(const char *file, int *reported)
{
FILE *fp = 0;
fp = fopen(file, "r");
if (!fp) {
if (!reported || *reported == 0) {
NORM_ERR("can't open %s: %s", file, strerror(errno));
if (reported) {
*reported = 1;
}
}
return NULL;
}
return fp;
}
void variable_substitute(const char *s, char *dest, unsigned int n)
{
while (*s && n > 1) {
if (*s == '$') {
s++;
if (*s != '$') {
char buf[256];
const char *a, *var;
unsigned int len;
/* variable is either $foo or ${foo} */
if (*s == '{') {
s++;
a = s;
while (*s && *s != '}') {
s++;
}
} else {
a = s;
while (*s && (isalnum((int) *s) || *s == '_')) {
s++;
}
}
/* copy variable to buffer and look it up */
len = (s - a > 255) ? 255 : (s - a);
strncpy(buf, a, len);
buf[len] = '\0';
if (*s == '}') {
s++;
}
var = getenv(buf);
if (var) {
/* add var to dest */
len = strlen(var);
if (len >= n) {
len = n - 1;
}
strncpy(dest, var, len);
dest += len;
n -= len;
}
continue;
}
}
*dest++ = *s++;
n--;
}
*dest = '\0';
}
void format_seconds(char *buf, unsigned int n, long seconds)
{
long days;
int hours, minutes;
if (times_in_seconds()) {
snprintf(buf, n, "%ld", seconds);
return;
}
days = seconds / 86400;
seconds %= 86400;
hours = seconds / 3600;
seconds %= 3600;
minutes = seconds / 60;
seconds %= 60;
if (days > 0) {
snprintf(buf, n, "%ldd %dh %dm", days, hours, minutes);
} else {
snprintf(buf, n, "%dh %dm %lds", hours, minutes, seconds);
}
}
void format_seconds_short(char *buf, unsigned int n, long seconds)
{
long days;
int hours, minutes;
if (times_in_seconds()) {
snprintf(buf, n, "%ld", seconds);
return;
}
days = seconds / 86400;
seconds %= 86400;
hours = seconds / 3600;
seconds %= 3600;
minutes = seconds / 60;
seconds %= 60;
if (days > 0) {
snprintf(buf, n, "%ldd %dh", days, hours);
} else if (hours > 0) {
snprintf(buf, n, "%dh %dm", hours, minutes);
} else {
snprintf(buf, n, "%dm %lds", minutes, seconds);
}
}
/* Linked list containing the functions to call upon each update interval.
* Populated while initialising text objects in construct_text_object(). */
struct update_cb {
struct update_cb *next;
void (*func)(void);
pthread_t thread;
sem_t start_wait, end_wait;
update_cb() : next(NULL), func(NULL) {}
/* set to 1 when starting the thread
* set to 0 to request thread termination */
volatile char running;
};
static struct update_cb update_cb_head;
static void *run_update_callback(void *) __attribute__((noreturn));
static int threading_started = 0;
/* Register an update callback. Don't allow duplicates, to minimise side
* effects and overhead. */
void add_update_callback(void (*func)(void))
{
struct update_cb *uc = &update_cb_head;
if (!func)
return;
while (uc->next) {
if (uc->next->func == func)
return;
uc = uc->next;
}
uc->next = new update_cb;
uc = uc->next;
memset(uc, 0, sizeof(struct update_cb));
uc->func = func;
sem_init(&uc->start_wait, 0, 0);
sem_init(&uc->end_wait, 0, 0);
if (threading_started) {
if (!uc->running) {
uc->running = 1;
pthread_create(&uc->thread, NULL, &run_update_callback, uc);
}
}
}
/* Free the list element uc and all decendants recursively. */
static void __free_update_callbacks(struct update_cb *uc)
{
if (uc->next)
__free_update_callbacks(uc->next);
if (uc->running) {
/* send cancellation request, then trigger and join the thread */
uc->running = 0;
sem_post(&uc->start_wait);
}
if (uc->thread && pthread_join(uc->thread, NULL)) {
NORM_ERR("Error destroying thread");
}
/* finally destroy the semaphores */
sem_destroy(&uc->start_wait);
sem_destroy(&uc->end_wait);
delete uc;
}
/* Free the whole list of update callbacks. */
void free_update_callbacks(void)
{
if (update_cb_head.next)
__free_update_callbacks(update_cb_head.next);
update_cb_head.next = NULL;
}
/* We cannot start threads before we forked to background, because the threads
* would remain in the wrong process. Because of that, add_update_callback()
* doesn't create threads before start_update_threading() is called.
* start_update_threading() starts all threads previously registered, and sets a
* flag so that future threads are automagically started by
* add_update_callback().
* This text is almost longer than the actual code.
*/
void start_update_threading(void)
{
struct update_cb *uc;
threading_started = 1;
for (uc = update_cb_head.next; uc; uc = uc->next) {
if (!uc->running) {
uc->running = 1;
pthread_create(&uc->thread, NULL, &run_update_callback, uc);
}
}
}
static void *run_update_callback(void *data)
{
struct update_cb *ucb = static_cast(data);
if (!ucb || !ucb->func) pthread_exit(NULL);
while (1) {
if (sem_wait(&ucb->start_wait)) pthread_exit(NULL);
if (ucb->running == 0) pthread_exit(NULL);
(*ucb->func)();
if (sem_post(&ucb->end_wait)) pthread_exit(NULL);
}
}
extern int no_buffers;
void update_stuff(void)
{
int i;
struct update_cb *uc;
/* clear speeds and up status in case device was removed and doesn't get
* updated */
#ifdef HAVE_OPENMP
#pragma omp parallel for schedule(dynamic,10)
#endif /* HAVE_OPENMP */
for (i = 0; i < MAX_NET_INTERFACES; i++) {
if (netstats[i].dev) {
netstats[i].up = 0;
netstats[i].recv_speed = 0.0;
netstats[i].trans_speed = 0.0;
}
}
prepare_update();
for (uc = update_cb_head.next; uc; uc = uc->next) {
if (sem_post(&uc->start_wait)) {
NORM_ERR("Semaphore error");
}
}
/* need to synchronise here, otherwise locking is needed (as data
* would be printed with some update callbacks still running) */
for (uc = update_cb_head.next; uc; uc = uc->next)
sem_wait(&uc->end_wait);
/* XXX: move the following into the update_meminfo() functions? */
if (no_buffers) {
info.mem -= info.bufmem;
info.memeasyfree += info.bufmem;
}
}
/* Ohkie to return negative values for temperatures */
int round_to_int_temp(float f)
{
if (f >= 0.0) {
return (int) (f + 0.5);
} else {
return (int) (f - 0.5);
}
}
/* Don't return negative values for cpugraph, bar, gauge, percentage.
* Causes unreasonable numbers to show */
unsigned int round_to_int(float f)
{
if (f >= 0.0) {
return (int) (f + 0.5);
} else {
return 0;
}
}
void scan_loadavg_arg(struct text_object *obj, const char *arg)
{
obj->data.i = 0;
if (arg && !arg[1] && isdigit(arg[0])) {
obj->data.i = atoi(arg);
if (obj->data.i > 3 || obj->data.i < 1) {
NORM_ERR("loadavg arg needs to be in range (1,3)");
obj->data.i = 0;
}
}
/* convert to array index (or the default (-1)) */
obj->data.i--;
}
void print_loadavg(struct text_object *obj, char *p, int p_max_size)
{
float *v = info.loadavg;
if (obj->data.i < 0) {
snprintf(p, p_max_size, "%.2f %.2f %.2f", v[0], v[1], v[2]);
} else {
snprintf(p, p_max_size, "%.2f", v[obj->data.i]);
}
}
#ifdef BUILD_X11
void scan_loadgraph_arg(struct text_object *obj, const char *arg)
{
char *buf = 0;
buf = scan_graph(obj, arg, 0);
free_and_zero(buf);
}
double loadgraphval(struct text_object *obj)
{
(void)obj;
return info.loadavg[0];
}
#endif /* BUILD_X11 */
uint8_t cpu_percentage(struct text_object *obj)
{
if (obj->data.i > info.cpu_count) {
NORM_ERR("obj->data.i %i info.cpu_count %i",
obj->data.i, info.cpu_count);
CRIT_ERR(NULL, NULL, "attempting to use more CPUs than you have!");
}
if (info.cpu_usage) {
return round_to_int(info.cpu_usage[obj->data.i] * 100.0);
} else {
return 0;
}
}
double cpu_barval(struct text_object *obj)
{
if (info.cpu_usage) {
return info.cpu_usage[obj->data.i];
} else {
return 0.;
}
}
#define PRINT_HR_GENERATOR(name) \
void print_##name(struct text_object *obj, char *p, int p_max_size) \
{ \
(void)obj; \
human_readable(info.name * 1024, p, p_max_size); \
}
PRINT_HR_GENERATOR(mem)
PRINT_HR_GENERATOR(memwithbuffers)
PRINT_HR_GENERATOR(memeasyfree)
PRINT_HR_GENERATOR(memfree)
PRINT_HR_GENERATOR(memmax)
PRINT_HR_GENERATOR(swap)
PRINT_HR_GENERATOR(swapfree)
PRINT_HR_GENERATOR(swapmax)
uint8_t mem_percentage(struct text_object *obj)
{
(void)obj;
return (info.memmax ? round_to_int(info.mem * 100 / info.memmax) : 0);
}
double mem_barval(struct text_object *obj)
{
(void)obj;
return info.memmax ? ((double)info.mem / info.memmax) : 0;
}
double mem_with_buffers_barval(struct text_object *obj)
{
(void)obj;
return info.memmax ? ((double)info.memwithbuffers / info.memmax) : 0;
}
uint8_t swap_percentage(struct text_object *obj)
{
(void)obj;
return (info.swapmax ? round_to_int(info.swap * 100 / info.swapmax) : 0);
}
double swap_barval(struct text_object *obj)
{
(void)obj;
return info.swapmax ? ((double)info.swap / info.swapmax) : 0;
}
void print_kernel(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
snprintf(p, p_max_size, "%s", info.uname_s.release);
}
void print_machine(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
snprintf(p, p_max_size, "%s", info.uname_s.machine);
}
void print_nodename(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
snprintf(p, p_max_size, "%s", info.uname_s.nodename);
}
void print_sysname(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
snprintf(p, p_max_size, "%s", info.uname_s.sysname);
}
void print_uptime(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
format_seconds(p, p_max_size, (int)info.uptime);
}
void print_uptime_short(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
format_seconds_short(p, p_max_size, (int)info.uptime);
}
void print_processes(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
spaced_print(p, p_max_size, "%hu", 4, info.procs);
}
void print_running_processes(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
spaced_print(p, p_max_size, "%hu", 4, info.run_procs);
}
void print_running_threads(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
spaced_print(p, p_max_size, "%hu", 4, info.run_threads);
}
void print_threads(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
spaced_print(p, p_max_size, "%hu", 4, info.threads);
}
void print_buffers(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
human_readable(info.buffers * 1024, p, p_max_size);
}
void print_cached(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
human_readable(info.cached * 1024, p, p_max_size);
}
void print_evaluate(struct text_object *obj, char *p, int p_max_size)
{
evaluate(obj->data.s, p, p_max_size);
}
int if_empty_iftest(struct text_object *obj)
{
std::vector buf(max_user_text);
int result = 1;
generate_text_internal(&(buf[0]), max_user_text, *obj->sub);
if (strlen(&(buf[0])) != 0) {
result = 0;
}
return result;
}
static int check_contains(char *f, char *s)
{
int ret = 0;
FILE *where = open_file(f, 0);
if (where) {
char buf1[256];
while (fgets(buf1, 256, where)) {
if (strstr(buf1, s)) {
ret = 1;
break;
}
}
fclose(where);
} else {
NORM_ERR("Could not open the file");
}
return ret;
}
int if_existing_iftest(struct text_object *obj)
{
char *spc;
int result = 1;
spc = strchr(obj->data.s, ' ');
if (!spc && access(obj->data.s, F_OK)) {
result = 0;
} else if (spc) {
*spc = '\0';
if (check_contains(obj->data.s, spc + 1))
result = 0;
*spc = ' ';
}
return result;
}
int if_running_iftest(struct text_object *obj)
{
#ifdef __linux__
if (!get_process_by_name(obj->data.s)) {
#else
if ((obj->data.s) && system(obj->data.s)) {
#endif
return 0;
}
return 1;
}
#ifndef __OpenBSD__
void print_acpitemp(struct text_object *obj, char *p, int p_max_size)
{
temp_print(p, p_max_size, get_acpi_temperature(obj->data.i), TEMP_CELSIUS);
}
void free_acpitemp(struct text_object *obj)
{
close(obj->data.i);
}
#endif /* !__OpenBSD__ */
void print_freq(struct text_object *obj, char *p, int p_max_size)
{
static int ok = 1;
if (ok) {
ok = get_freq(p, p_max_size, "%.0f", 1, obj->data.i);
}
}
void print_freq_g(struct text_object *obj, char *p, int p_max_size)
{
static int ok = 1;
if (ok) {
#ifndef __OpenBSD__
ok = get_freq(p, p_max_size, "%'.2f", 1000, obj->data.i);
#else
/* OpenBSD has no such flag (SUSv2) */
ok = get_freq(p, p_max_size, "%.2f", 1000, obj->data.i);
#endif /* __OpenBSD */
}
}
#ifndef __OpenBSD__
void print_acpifan(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
get_acpi_fan(p, p_max_size);
}
void print_acpiacadapter(struct text_object *obj, char *p, int p_max_size)
{
get_acpi_ac_adapter(p, p_max_size, (const char *)obj->data.opaque);
}
void print_battery(struct text_object *obj, char *p, int p_max_size)
{
get_battery_stuff(p, p_max_size, obj->data.s, BATTERY_STATUS);
}
void print_battery_time(struct text_object *obj, char *p, int p_max_size)
{
get_battery_stuff(p, p_max_size, obj->data.s, BATTERY_TIME);
}
uint8_t battery_percentage(struct text_object *obj)
{
return get_battery_perct(obj->data.s);
}
void print_battery_short(struct text_object *obj, char *p, int p_max_size)
{
get_battery_short_status(p, p_max_size, obj->data.s);
}
#endif /* !__OpenBSD__ */
void print_blink(struct text_object *obj, char *p, int p_max_size)
{
//blinking like this can look a bit ugly if the chars in the font don't have the same width
std::vector buf(max_user_text);
static int visible = 1;
static int last_len = 0;
int i;
if (visible) {
generate_text_internal(&(buf[0]), max_user_text, *obj->sub);
last_len = strlen(&(buf[0]));
} else {
for (i = 0; i < last_len; i++)
buf[i] = ' ';
}
snprintf(p, p_max_size, "%s", &(buf[0]));
visible = !visible;
}
void print_include(struct text_object *obj, char *p, int p_max_size)
{
std::vector buf(max_user_text);
if (!obj->sub)
return;
generate_text_internal(&(buf[0]), max_user_text, *obj->sub);
snprintf(p, p_max_size, "%s", &(buf[0]));
}
void print_to_bytes(struct text_object *obj, char *p, int p_max_size)
{
std::vector buf(max_user_text);
long long bytes;
char unit[16]; // 16 because we can also have long names (like mega-bytes)
generate_text_internal(&(buf[0]), max_user_text, *obj->sub);
if(sscanf(&(buf[0]), "%lli%s", &bytes, unit) == 2 && strlen(unit) < 16){
if(strncasecmp("b", unit, 1) == 0) snprintf(&(buf[0]), max_user_text, "%lli", bytes);
else if(strncasecmp("k", unit, 1) == 0) snprintf(&(buf[0]), max_user_text, "%lli", bytes * 1024);
else if(strncasecmp("m", unit, 1) == 0) snprintf(&(buf[0]), max_user_text, "%lli", bytes * 1024 * 1024);
else if(strncasecmp("g", unit, 1) == 0) snprintf(&(buf[0]), max_user_text, "%lli", bytes * 1024 * 1024 * 1024);
else if(strncasecmp("t", unit, 1) == 0) snprintf(&(buf[0]), max_user_text, "%lli", bytes * 1024 * 1024 * 1024 * 1024);
}
snprintf(p, p_max_size, "%s", &(buf[0]));
}
void print_updates(struct text_object *obj, char *p, int p_max_size)
{
(void)obj;
snprintf(p, p_max_size, "%d", get_total_updates());
}
int updatenr_iftest(struct text_object *obj)
{
if (get_total_updates() % get_updatereset() != obj->data.i - 1)
return 0;
return 1;
}